15f270659SKonstantin Belousov 2193d9e76SEnji Cooper.PATH: ${SRCTOP}/sys/crypto/aesni 3*0b57cec5SDimitry Andric.PATH: ${SRCTOP}/contrib/llvm-project/clang/lib/Headers 45f270659SKonstantin Belousov 55f270659SKonstantin BelousovKMOD= aesni 6ff6c7bf5SJohn-Mark GurneySRCS= aesni.c 7ff6c7bf5SJohn-Mark GurneySRCS+= aeskeys_${MACHINE_CPUARCH}.S 85f270659SKonstantin BelousovSRCS+= device_if.h bus_if.h opt_bus.h cryptodev_if.h 95f270659SKonstantin Belousov 107cff9f37SSean Eric FaganOBJS+= aesni_ghash.o aesni_wrap.o aesni_ccm.o 11fe182ba1SConrad MeyerOBJS+= intel_sha1.o intel_sha256.o 12ff6c7bf5SJohn-Mark Gurney 13ff6c7bf5SJohn-Mark Gurney# Remove -nostdinc so we can get the intrinsics. 1408fca7a5SJohn-Mark Gurneyaesni_ghash.o: aesni_ghash.c 157cff9f37SSean Eric Fagan ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 167cff9f37SSean Eric Fagan -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC} 177cff9f37SSean Eric Fagan ${CTFCONVERT_CMD} 187cff9f37SSean Eric Fagan 197cff9f37SSean Eric Faganaesni_ccm.o: aesni_ccm.c 2008fca7a5SJohn-Mark Gurney ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 2108fca7a5SJohn-Mark Gurney -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC} 2208fca7a5SJohn-Mark Gurney ${CTFCONVERT_CMD} 2308fca7a5SJohn-Mark Gurney 24ff6c7bf5SJohn-Mark Gurneyaesni_wrap.o: aesni_wrap.c 25ff6c7bf5SJohn-Mark Gurney ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 2608fca7a5SJohn-Mark Gurney -mmmx -msse -msse4 -maes ${.IMPSRC} 27ff6c7bf5SJohn-Mark Gurney ${CTFCONVERT_CMD} 28ff6c7bf5SJohn-Mark Gurney 29fe182ba1SConrad Meyerintel_sha1.o: intel_sha1.c 30fe182ba1SConrad Meyer ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 31fe182ba1SConrad Meyer -mmmx -msse -msse4 -msha ${.IMPSRC} 32fe182ba1SConrad Meyer ${CTFCONVERT_CMD} 33fe182ba1SConrad Meyer 34fe182ba1SConrad Meyerintel_sha256.o: intel_sha256.c 35fe182ba1SConrad Meyer ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \ 36fe182ba1SConrad Meyer -mmmx -msse -msse4 -msha ${.IMPSRC} 37fe182ba1SConrad Meyer ${CTFCONVERT_CMD} 38fe182ba1SConrad Meyer 3964ff224dSJohn-Mark Gurneyaesni_ghash.o: aesni.h 4064ff224dSJohn-Mark Gurneyaesni_wrap.o: aesni.h 417cff9f37SSean Eric Faganaesni_ccm.o: aesni.h 42fe182ba1SConrad Meyerintel_sha1.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h 43fe182ba1SConrad Meyerintel_sha256.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h 4464ff224dSJohn-Mark Gurney 455f270659SKonstantin Belousov.include <bsd.kmod.mk> 46c234c2deSDimitry Andric 47c234c2deSDimitry AndricCWARNFLAGS.aesni_ghash.c= ${NO_WCAST_QUAL} 48c234c2deSDimitry AndricCWARNFLAGS.aesni_wrap.c= ${NO_WCAST_QUAL} 49