Page MenuHomeFreeBSD
Differential D18520 Diff 51945 sys/modules/aesni/Makefile

Changeset View

Standalone View

View Options

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} \
cemUnsubmitted
Done
Inline Actions

I think this comment is stale and refers to gcc4. x86 hasn't used gcc4 since BSD9 or 10. gcc8's manual page documents -mpclmul, and I build all of my kernels with GCC, including aesni.ko, so... maybe just drop the comment along with the original.

cem: I think this comment is stale and refers to gcc4. x86 hasn't used gcc4 since BSD9 or 10.
-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}