1193d9e76SEnji Cooper.PATH: ${SRCTOP}/sys/crypto/aesni 2*0b57cec5SDimitry Andric.PATH: ${SRCTOP}/contrib/llvm-project/clang/lib/Headers 35f270659SKonstantin Belousov 45f270659SKonstantin BelousovKMOD= aesni 5ff6c7bf5SJohn-Mark GurneySRCS= aesni.c 6ff6c7bf5SJohn-Mark GurneySRCS+= aeskeys_${MACHINE_CPUARCH}.S 75f270659SKonstantin BelousovSRCS+= device_if.h bus_if.h opt_bus.h cryptodev_if.h 85f270659SKonstantin Belousov 97cff9f37SSean Eric FaganOBJS+= aesni_ghash.o aesni_wrap.o aesni_ccm.o 10fe182ba1SConrad MeyerOBJS+= intel_sha1.o intel_sha256.o 11ff6c7bf5SJohn-Mark Gurney 12ff6c7bf5SJohn-Mark Gurney# Remove -nostdinc so we can get the intrinsics. 1308fca7a5SJohn-Mark Gurneyaesni_ghash.o: aesni_ghash.c 147cff9f37SSean Eric Fagan ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 157cff9f37SSean Eric Fagan -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC} 167cff9f37SSean Eric Fagan ${CTFCONVERT_CMD} 177cff9f37SSean Eric Fagan 187cff9f37SSean Eric Faganaesni_ccm.o: aesni_ccm.c 1908fca7a5SJohn-Mark Gurney ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 2008fca7a5SJohn-Mark Gurney -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC} 2108fca7a5SJohn-Mark Gurney ${CTFCONVERT_CMD} 2208fca7a5SJohn-Mark Gurney 23ff6c7bf5SJohn-Mark Gurneyaesni_wrap.o: aesni_wrap.c 24ff6c7bf5SJohn-Mark Gurney ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 2508fca7a5SJohn-Mark Gurney -mmmx -msse -msse4 -maes ${.IMPSRC} 26ff6c7bf5SJohn-Mark Gurney ${CTFCONVERT_CMD} 27ff6c7bf5SJohn-Mark Gurney 28fe182ba1SConrad Meyerintel_sha1.o: intel_sha1.c 29fe182ba1SConrad Meyer ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 30fe182ba1SConrad Meyer -mmmx -msse -msse4 -msha ${.IMPSRC} 31fe182ba1SConrad Meyer ${CTFCONVERT_CMD} 32fe182ba1SConrad Meyer 33fe182ba1SConrad Meyerintel_sha256.o: intel_sha256.c 34fe182ba1SConrad Meyer ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 35fe182ba1SConrad Meyer -mmmx -msse -msse4 -msha ${.IMPSRC} 36fe182ba1SConrad Meyer ${CTFCONVERT_CMD} 37fe182ba1SConrad Meyer 3864ff224dSJohn-Mark Gurneyaesni_ghash.o: aesni.h 3964ff224dSJohn-Mark Gurneyaesni_wrap.o: aesni.h 407cff9f37SSean Eric Faganaesni_ccm.o: aesni.h 41fe182ba1SConrad Meyerintel_sha1.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h 42fe182ba1SConrad Meyerintel_sha256.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h 4364ff224dSJohn-Mark Gurney 445f270659SKonstantin Belousov.include <bsd.kmod.mk> 45c234c2deSDimitry Andric 46c234c2deSDimitry AndricCWARNFLAGS.aesni_ghash.c= ${NO_WCAST_QUAL} 47c234c2deSDimitry AndricCWARNFLAGS.aesni_wrap.c= ${NO_WCAST_QUAL} 48