sys/modules/aesni/Makefile

   1 # $FreeBSD$
   2
   3 .PATH: ${SRCTOP}/sys/crypto/aesni
   4 .PATH: ${SRCTOP}/contrib/llvm-project/clang/lib/Headers
   5
   6 KMOD=   aesni
   7 SRCS=   aesni.c
   8 SRCS+=  aeskeys_${MACHINE_CPUARCH}.S
   9 SRCS+=  device_if.h bus_if.h opt_bus.h cryptodev_if.h
  10
  11 OBJS+=  aesni_ghash.o aesni_wrap.o aesni_ccm.o
  12 OBJS+=  intel_sha1.o intel_sha256.o
  13
  14 # Remove -nostdinc so we can get the intrinsics.
  15 aesni_ghash.o: aesni_ghash.c
  16         ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
  17              -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC}
  18         ${CTFCONVERT_CMD}
  19
  20 aesni_ccm.o: aesni_ccm.c
  21         ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
  22              -mmmx -msse -msse4 -maes -mpclmul ${.IMPSRC}
  23         ${CTFCONVERT_CMD}
  24
  25 aesni_wrap.o: aesni_wrap.c
  26         ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
  27              -mmmx -msse -msse4 -maes ${.IMPSRC}
  28         ${CTFCONVERT_CMD}
  29
  30 intel_sha1.o: intel_sha1.c
  31         ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
  32              -mmmx -msse -msse4 -msha ${.IMPSRC}
  33         ${CTFCONVERT_CMD}
  34
  35 intel_sha256.o: intel_sha256.c
  36         ${CC} -c ${CFLAGS:C/^-O2$/-O3/:N-nostdinc} ${WERROR} ${PROF} \
  37              -mmmx -msse -msse4 -msha ${.IMPSRC}
  38         ${CTFCONVERT_CMD}
  39
  40 aesni_ghash.o: aesni.h
  41 aesni_wrap.o: aesni.h
  42 aesni_ccm.o: aesni.h
  43 intel_sha1.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h
  44 intel_sha256.o: sha_sse.h immintrin.h shaintrin.h tmmintrin.h xmmintrin.h
  45
  46 .include <bsd.kmod.mk>
  47
  48 CWARNFLAGS.aesni_ghash.c=       ${NO_WCAST_QUAL}
  49 CWARNFLAGS.aesni_wrap.c=        ${NO_WCAST_QUAL}