ossl: Move arm_arch.h to a common subdirectoryOpenSSL itself keeps only a single copy of this header. Do the same insys/crypto/openssl to avoid the extra maintenance burden. This requiresadjust
ossl: Move arm_arch.h to a common subdirectoryOpenSSL itself keeps only a single copy of this header. Do the same insys/crypto/openssl to avoid the extra maintenance burden. This requiresadjusting the include paths for generated asm files.No functional change intended.Reported by: jrtc27Reviewed by: jhbMFC after: 3 monthsDifferential Revision: https://reviews.freebsd.org/D42866(cherry picked from commit e655cc70dfcda5cfedb5a1d9bef1e87d55519f64)
show more ...
sys: Remove $FreeBSD$: one-line sh patternRemove /^\s*#[#!]?\s*\$FreeBSD\$.*$\n/
Remove nonexistent include path for arm64 crypto files.Reviewed by: emasteDifferential Revision: https://reviews.freebsd.org/D31932
armv8crypto: add AES-GCM supportAdd support for AES-GCM using OpenSSL's accelerated routines.Reviewed by: jhbDifferential Revision: https://reviews.freebsd.org/D27454Sponsored by: Ampere Comput
armv8crypto: add AES-GCM supportAdd support for AES-GCM using OpenSSL's accelerated routines.Reviewed by: jhbDifferential Revision: https://reviews.freebsd.org/D27454Sponsored by: Ampere ComputingSubmitted by: Klara, Inc.
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
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