Changeset View
Changeset View
Standalone View
Standalone View
head/sys/modules/aesni/Makefile
| # $FreeBSD$ | # $FreeBSD$ | ||||
| .PATH: ${SRCTOP}/sys/crypto/aesni | .PATH: ${SRCTOP}/sys/crypto/aesni | ||||
| .PATH: ${SRCTOP}/contrib/llvm/tools/clang/lib/Headers | .PATH: ${SRCTOP}/contrib/llvm/tools/clang/lib/Headers | ||||
| KMOD= aesni | KMOD= aesni | ||||
| SRCS= aesni.c | SRCS= aesni.c | ||||
| SRCS+= aeskeys_${MACHINE_CPUARCH}.S | SRCS+= aeskeys_${MACHINE_CPUARCH}.S | ||||
| SRCS+= device_if.h bus_if.h opt_bus.h cryptodev_if.h | SRCS+= device_if.h bus_if.h opt_bus.h cryptodev_if.h | ||||
| OBJS+= aesni_ghash.o aesni_wrap.o | OBJS+= aesni_ghash.o aesni_wrap.o aesni_ccm.o | ||||
| OBJS+= intel_sha1.o intel_sha256.o | OBJS+= intel_sha1.o intel_sha256.o | ||||
| # Remove -nostdinc so we can get the intrinsics. | # Remove -nostdinc so we can get the intrinsics. | ||||
| aesni_ghash.o: aesni_ghash.c | aesni_ghash.o: aesni_ghash.c | ||||
| # XXX - gcc won't understand -mpclmul | |||||
| ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ||||
| -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC} | -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC} | ||||
| ${CTFCONVERT_CMD} | ${CTFCONVERT_CMD} | ||||
| aesni_ccm.o: aesni_ccm.c | |||||
| ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | |||||
| -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC} | |||||
| ${CTFCONVERT_CMD} | |||||
| aesni_wrap.o: aesni_wrap.c | aesni_wrap.o: aesni_wrap.c | ||||
| ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ||||
| -mmmx -msse -msse4 -maes ${.IMPSRC} | -mmmx -msse -msse4 -maes ${.IMPSRC} | ||||
| ${CTFCONVERT_CMD} | ${CTFCONVERT_CMD} | ||||
| intel_sha1.o: intel_sha1.c | intel_sha1.o: intel_sha1.c | ||||
| ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ||||
| -mmmx -msse -msse4 -msha ${.IMPSRC} | -mmmx -msse -msse4 -msha ${.IMPSRC} | ||||
| ${CTFCONVERT_CMD} | ${CTFCONVERT_CMD} | ||||
| intel_sha256.o: intel_sha256.c | intel_sha256.o: intel_sha256.c | ||||
| ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ | ||||
| -mmmx -msse -msse4 -msha ${.IMPSRC} | -mmmx -msse -msse4 -msha ${.IMPSRC} | ||||
| ${CTFCONVERT_CMD} | ${CTFCONVERT_CMD} | ||||
| aesni_ghash.o: aesni.h | aesni_ghash.o: aesni.h | ||||
| aesni_wrap.o: aesni.h | aesni_wrap.o: aesni.h | ||||
| aesni_ccm.o: aesni.h | |||||
| intel_sha1.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.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 | intel_sha256.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h | ||||
| .include <bsd.kmod.mk> | .include <bsd.kmod.mk> | ||||
| CWARNFLAGS.aesni_ghash.c= ${NO_WCAST_QUAL} | CWARNFLAGS.aesni_ghash.c= ${NO_WCAST_QUAL} | ||||
| CWARNFLAGS.aesni_wrap.c= ${NO_WCAST_QUAL} | CWARNFLAGS.aesni_wrap.c= ${NO_WCAST_QUAL} | ||||