|
Revision tags: release/12.4.0, release/13.1.0, release/12.3.0, release/13.0.0 |
|
| #
f76393a6 |
| 13-Jan-2021 |
Oleksandr Tymoshenko <[email protected]> |
armv8crypto: add AES-GCM support
Add support for AES-GCM using OpenSSL's accelerated routines.
Reviewed by: jhb Differential Revision: https://reviews.freebsd.org/D27454 Sponsored by: Ampere Comput
armv8crypto: add AES-GCM support
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. Approved by: re (kib)
(cherry picked from commit ed9b7f4414663703e0e9581a730c4bdfaca5687f)
show more ...
|
|
Revision tags: release/12.2.0, release/11.4.0, release/12.1.0, release/11.3.0, release/12.0.0 |
|
| #
a9dc38de |
| 16-Jul-2018 |
Andrew Turner <[email protected]> |
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 th
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
show more ...
|
|
Revision tags: release/11.2.0, release/10.4.0 |
|
| #
3f32b92b |
| 19-Aug-2017 |
Andrew Turner <[email protected]> |
Use armv8-a in -march, it is accepted by both clang and gcc.
Sponsored by: DARPA, AFRL
|
|
Revision tags: release/11.1.0 |
|
| #
193d9e76 |
| 04-Mar-2017 |
Enji Cooper <[email protected]> |
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
|
| #
d6699d29 |
| 21-Nov-2016 |
Andrew Turner <[email protected]> |
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
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
show more ...
|