4 Commits

Author	SHA1	Message	Date
Andrew Turner	a9dc38def4	Create an empty stdint.h for arm_neon.h to include. ... The armv8crypto module includes arm_neon.h for the compiler intrinsic functions. This includes the userland stdint.h file that doesn't exist in the kernel. Fix this by providing an empty stdint.h to be used when we include arm_neon.h. Sponsored by: DARPA, AFRL Differential Revision: https://reviews.freebsd.org/D16254	2018-07-16 15:39:33 +00:00
Andrew Turner	3f32b92b1d	Use armv8-a in -march, it is accepted by both clang and gcc. ... Sponsored by: DARPA, AFRL	2017-08-19 17:15:40 +00:00
Enji Cooper	193d9e768b	sys/modules: normalize .CURDIR-relative paths to SRCTOP ... This simplifies make output/logic Tested with: `cd sys/modules; make ALL_MODULES=` on amd64 MFC after: 1 month Sponsored by: Dell EMC Isilon	2017-03-04 10:10:17 +00:00
Andrew Turner	d6699d292b	Add accelerated AES with using the ARMv8 crypto instructions. This is based ... on the AES-NI code, and modified as needed for use on ARMv8. When loaded the driver will check the appropriate field in the id_aa64isar0_el1 register to see if AES is supported, and if so the probe function will signal the driver should attach. With this I have seen up to 2000Mb/s from the cryptotest test with a single thread on a ThunderX Pass 2.0. Reviewed by: imp Obtained from: ABT Systems Ltd MFC after: 1 week Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D8297	2016-11-21 11:18:00 +00:00