cccc969bc7
We can't modify vendor code so there's no signal in warnings from it. Similarly -Waddress-of-packed-member is not useful on networking code as access to packed structures is fundamental to its operation.
92 lines
2.3 KiB
Makefile
92 lines
2.3 KiB
Makefile
# $FreeBSD$
|
|
|
|
.PATH: ${SRCTOP}/sys/contrib/libb2
|
|
.PATH: ${SRCTOP}/sys/crypto/blake2
|
|
.PATH: ${SRCTOP}/sys/opencrypto
|
|
.PATH: ${SRCTOP}/contrib/llvm/tools/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
|