aboutsummaryrefslogtreecommitdiff
path: root/sys/modules/armv8crypto
Commit message (Collapse)AuthorAgeFilesLines
* ossl: Move arm_arch.h to a common subdirectoryMark Johnston2023-12-041-1/+2
| | | | | | | | | | | | | OpenSSL itself keeps only a single copy of this header. Do the same in sys/crypto/openssl to avoid the extra maintenance burden. This requires adjusting the include paths for generated asm files. No functional change intended. Reported by: jrtc27 Reviewed by: jhb MFC after: 3 months Differential Revision: https://reviews.freebsd.org/D42866
* sys: Remove $FreeBSD$: one-line sh patternWarner Losh2023-08-161-1/+0
| | | | Remove /^\s*#[#!]?\s*\$FreeBSD\$.*$\n/
* Remove nonexistent include path for arm64 crypto files.John Baldwin2021-09-151-2/+0
| | | | | Reviewed by: emaste Differential Revision: https://reviews.freebsd.org/D31932
* armv8crypto: add AES-GCM supportOleksandr Tymoshenko2021-01-221-1/+18
| | | | | | | | | Add support for AES-GCM using OpenSSL's accelerated routines. Reviewed by: jhb Differential Revision: https://reviews.freebsd.org/D27454 Sponsored by: Ampere Computing Submitted by: Klara, Inc.
* Create an empty stdint.h for arm_neon.h to include.Andrew Turner2018-07-161-0/+1
| | | | | | | | | | | | | 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 Notes: svn path=/head/; revision=336348
* Use armv8-a in -march, it is accepted by both clang and gcc.Andrew Turner2017-08-191-1/+1
| | | | | | | Sponsored by: DARPA, AFRL Notes: svn path=/head/; revision=322696
* sys/modules: normalize .CURDIR-relative paths to SRCTOPEnji Cooper2017-03-041-1/+1
| | | | | | | | | | | This simplifies make output/logic Tested with: `cd sys/modules; make ALL_MODULES=` on amd64 MFC after: 1 month Sponsored by: Dell EMC Isilon Notes: svn path=/head/; revision=314651
* Add accelerated AES with using the ARMv8 crypto instructions. This is basedAndrew Turner2016-11-211-0/+20
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 Notes: svn path=/head/; revision=308921