Create an empty stdint.h for arm_neon.h to include.The armv8crypto module includes arm_neon.h for the compiler intrinsicfunctions. This includes the userland stdint.h file that doesn't exist inth
Create an empty stdint.h for arm_neon.h to include.The armv8crypto module includes arm_neon.h for the compiler intrinsicfunctions. This includes the userland stdint.h file that doesn't exist inthe kernel. Fix this by providing an empty stdint.h to be used when weinclude arm_neon.h.Sponsored by: DARPA, AFRLDifferential Revision: https://reviews.freebsd.org/D16254
show more ...
Use armv8-a in -march, it is accepted by both clang and gcc.Sponsored by: DARPA, AFRL
sys/modules: normalize .CURDIR-relative paths to SRCTOPThis simplifies make output/logicTested with: `cd sys/modules; make ALL_MODULES=` on amd64MFC after: 1 monthSponsored by: Dell EMC Isilon
Add accelerated AES with using the ARMv8 crypto instructions. This is basedon the AES-NI code, and modified as needed for use on ARMv8. When loadedthe driver will check the appropriate field in the
Add accelerated AES with using the ARMv8 crypto instructions. This is basedon the AES-NI code, and modified as needed for use on ARMv8. When loadedthe driver will check the appropriate field in the id_aa64isar0_el1register to see if AES is supported, and if so the probe function willsignal the driver should attach.With this I have seen up to 2000Mb/s from the cryptotest test with a singlethread on a ThunderX Pass 2.0.Reviewed by: impObtained from: ABT Systems LtdMFC after: 1 weekSponsored by: The FreeBSD FoundationDifferential Revision: https://reviews.freebsd.org/D8297