123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990 |
- .PATH: ${SRCTOP}/sys/contrib/libb2
- .PATH: ${SRCTOP}/sys/crypto/blake2
- .PATH: ${SRCTOP}/sys/opencrypto
- .PATH: ${SRCTOP}/contrib/llvm-project/clang/lib/Headers
- KMOD = blake2
- # Vendor sources
- SRCS += blake2.h
- SRCS += blake2-impl.h
- SRCS += blake2-config.h
- SRCS += blake2-dispatch.c
- SRCS += blake2bp.c
- SRCS += blake2sp.c
- CFLAGS += -I${SRCTOP}/sys/contrib/libb2
- CFLAGS += -I${SRCTOP}/sys/crypto/blake2
- # x86 specific optimization headers:
- SRCS += blake2b-load-sse2.h
- SRCS += blake2b-load-sse41.h
- SRCS += blake2b-round.h
- SRCS += blake2s-load-sse2.h
- SRCS += blake2s-load-sse41.h
- SRCS += blake2s-load-xop.h
- SRCS += blake2s-round.h
- # C files to build a dispatched fat implementation on x86
- SRCS_IN += blake2b-sse2.c
- SRCS_IN += blake2b-ssse3.c
- SRCS_IN += blake2b-sse41.c
- SRCS_IN += blake2b-avx.c
- SRCS_IN += blake2b-xop.c
- SRCS_IN += blake2s-sse2.c
- SRCS_IN += blake2s-ssse3.c
- SRCS_IN += blake2s-sse41.c
- SRCS_IN += blake2s-avx.c
- SRCS_IN += blake2s-xop.c
- OBJS+= ${SRCS_IN:S/.c/.o/g}
- CFLAGS.blake2b-sse2.c += -DSUFFIX=_sse2 -msse2
- CFLAGS.blake2s-sse2.c += -DSUFFIX=_sse2 -msse2
- CFLAGS.blake2b-ssse3.c += -DSUFFIX=_ssse3 -msse2 -mssse3
- CFLAGS.blake2s-ssse3.c += -DSUFFIX=_ssse3 -msse2 -mssse3
- CFLAGS.blake2b-sse41.c += -DSUFFIX=_sse41 -msse2 -mssse3 -msse4.1
- CFLAGS.blake2s-sse41.c += -DSUFFIX=_sse41 -msse2 -mssse3 -msse4.1
- CFLAGS.blake2b-avx.c += -DSUFFIX=_avx -msse2 -mssse3 -msse4.1 -mavx
- CFLAGS.blake2s-avx.c += -DSUFFIX=_avx -msse2 -mssse3 -msse4.1 -mavx
- CFLAGS.blake2b-xop.c += -DSUFFIX=_xop -msse2 -mssse3 -msse4.1 -mavx -mxop
- CFLAGS.blake2s-xop.c += -DSUFFIX=_xop -msse2 -mssse3 -msse4.1 -mavx -mxop
- .for src in ${SRCS_IN}
- ${src:S/.c/.o/}: ${src}
- ${CC} -c ${CFLAGS:N-nostdinc} ${CFLAGS.${src}} ${WERROR} ${PROF} \
- -D_MM_MALLOC_H_INCLUDED -Wno-unused-function ${.IMPSRC}
- ${CTFCONVERT_CMD}
- ${src:S/.c/.o/}: intrin.h emmintrin.h tmmintrin.h smmintrin.h immintrin.h \
- x86intrin.h ${SRCS:M*.h}
- .endfor
- # FreeBSD-specific sources:
- SRCS += blake2_kfreebsd.h
- SRCS += config.h
- SRCS += stddef.h
- SRCS += stdint.h
- SRCS += stdio.h
- SRCS += stdlib.h
- SRCS += string.h
- SRCS += blake2_cryptodev.c
- SRCS += opt_param.h cryptodev_if.h bus_if.h device_if.h
- WARNS ?= 6
- .include <bsd.kmod.mk>
- CWARNFLAGS.blake2-dispatch.c += -Wno-unused-const-variable
- CWARNFLAGS.blake2s-ref.c += -Wno-cast-qual -Wno-unused-function
- CWARNFLAGS += -Wno-cast-qual
|