3 .PATH: ${SRCTOP}/sys/crypto/aesni
4 .PATH: ${SRCTOP}/contrib/llvm/tools/clang/lib/Headers
8 SRCS+= aeskeys_${MACHINE_CPUARCH}.S
9 SRCS+= device_if.h bus_if.h opt_bus.h cryptodev_if.h
11 OBJS+= aesni_ghash.o aesni_wrap.o aesni_ccm.o
12 OBJS+= intel_sha1.o intel_sha256.o
14 # Remove -nostdinc so we can get the intrinsics.
15 aesni_ghash.o: aesni_ghash.c
16 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
17 -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC}
20 aesni_ccm.o: aesni_ccm.c
21 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
22 -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC}
25 aesni_wrap.o: aesni_wrap.c
26 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
27 -mmmx -msse -msse4 -maes ${.IMPSRC}
30 intel_sha1.o: intel_sha1.c
31 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
32 -mmmx -msse -msse4 -msha ${.IMPSRC}
35 intel_sha256.o: intel_sha256.c
36 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
37 -mmmx -msse -msse4 -msha ${.IMPSRC}
40 aesni_ghash.o: aesni.h
43 intel_sha1.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h
44 intel_sha256.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h
46 .include <bsd.kmod.mk>
48 CWARNFLAGS.aesni_ghash.c= ${NO_WCAST_QUAL}
49 CWARNFLAGS.aesni_wrap.c= ${NO_WCAST_QUAL}