Differential D19298 Diff 55565 sys/modules/aesni/Makefile

Changeset View

Standalone View

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
				cemUnsubmitted Done Inline Actions I think this comment is stale in both places — aesni.ko builds fine with GCC xtoolchain, and aesni.ko is useless on platforms that are still on ancient gcc4. cem: I think this comment is stale in both places — aesni.ko builds fine with GCC xtoolchain, and…
				sefAuthorUnsubmitted Done Inline Actions Well, I just copied it, but I've removed both now. sef: Well, I just copied it, but I've removed both now.
				cemUnsubmitted Not Done Inline Actions Right, thanks. cem: Right, thanks.
	${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}