diff options
| author | Conrad Meyer <cem@FreeBSD.org> | 2017-09-26 23:12:32 +0000 |
|---|---|---|
| committer | Conrad Meyer <cem@FreeBSD.org> | 2017-09-26 23:12:32 +0000 |
| commit | fe182ba1d010bb944c16cf04483da8e380dce1cb (patch) | |
| tree | 4339c4b8ae3cbb748c5151908f628c552fd4e615 /sys/modules/aesni | |
| parent | 119bdf3b3abd18520e44ebdd3b64496bf84e2747 (diff) | |
Notes
Diffstat (limited to 'sys/modules/aesni')
| -rw-r--r-- | sys/modules/aesni/Makefile | 14 |
1 files changed, 14 insertions, 0 deletions
diff --git a/sys/modules/aesni/Makefile b/sys/modules/aesni/Makefile index 82f6d1178ff8..56500faa8e4a 100644 --- a/sys/modules/aesni/Makefile +++ b/sys/modules/aesni/Makefile @@ -1,6 +1,7 @@ # $FreeBSD$ .PATH: ${SRCTOP}/sys/crypto/aesni +.PATH: ${SRCTOP}/contrib/llvm/tools/clang/lib/Headers KMOD= aesni SRCS= aesni.c @@ -8,6 +9,7 @@ SRCS+= aeskeys_${MACHINE_CPUARCH}.S SRCS+= device_if.h bus_if.h opt_bus.h cryptodev_if.h OBJS+= aesni_ghash.o aesni_wrap.o +OBJS+= intel_sha1.o intel_sha256.o # Remove -nostdinc so we can get the intrinsics. aesni_ghash.o: aesni_ghash.c @@ -21,8 +23,20 @@ aesni_wrap.o: aesni_wrap.c -mmmx -msse -msse4 -maes ${.IMPSRC} ${CTFCONVERT_CMD} +intel_sha1.o: intel_sha1.c + ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ + -mmmx -msse -msse4 -msha ${.IMPSRC} + ${CTFCONVERT_CMD} + +intel_sha256.o: intel_sha256.c + ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ + -mmmx -msse -msse4 -msha ${.IMPSRC} + ${CTFCONVERT_CMD} + aesni_ghash.o: aesni.h aesni_wrap.o: aesni.h +intel_sha1.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h +intel_sha256.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h .include <bsd.kmod.mk> |