1 # $FreeBSD: releng/12.0/sys/modules/aesni/Makefile 324037 2017-09-26 23:12:32Z cem $
2
3 .PATH: ${SRCTOP}/sys/crypto/aesni
4 .PATH: ${SRCTOP}/contrib/llvm/tools/clang/lib/Headers
5
6 KMOD= aesni
7 SRCS= aesni.c
8 SRCS+= aeskeys_${MACHINE_CPUARCH}.S
9 SRCS+= device_if.h bus_if.h opt_bus.h cryptodev_if.h
10
11 OBJS+= aesni_ghash.o aesni_wrap.o
12 OBJS+= intel_sha1.o intel_sha256.o
13
14 # Remove -nostdinc so we can get the intrinsics.
15 aesni_ghash.o: aesni_ghash.c
16 # XXX - gcc won't understand -mpclmul
17 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
18 -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC}
19 ${CTFCONVERT_CMD}
20
21 aesni_wrap.o: aesni_wrap.c
22 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
23 -mmmx -msse -msse4 -maes ${.IMPSRC}
24 ${CTFCONVERT_CMD}
25
26 intel_sha1.o: intel_sha1.c
27 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
28 -mmmx -msse -msse4 -msha ${.IMPSRC}
29 ${CTFCONVERT_CMD}
30
31 intel_sha256.o: intel_sha256.c
32 ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
33 -mmmx -msse -msse4 -msha ${.IMPSRC}
34 ${CTFCONVERT_CMD}
35
36 aesni_ghash.o: aesni.h
37 aesni_wrap.o: aesni.h
38 intel_sha1.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h
39 intel_sha256.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h
40
41 .include <bsd.kmod.mk>
42
43 CWARNFLAGS.aesni_ghash.c= ${NO_WCAST_QUAL}
44 CWARNFLAGS.aesni_wrap.c= ${NO_WCAST_QUAL}
Cache object: 980605742d6d598748bf7c4bd4924052
|