| #
e655cc70 |
| 04-Dec-2023 |
Mark Johnston <markj@FreeBSD.org> |
ossl: Move arm_arch.h to a common subdirectory
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
adjust
ossl: Move arm_arch.h to a common subdirectory
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
show more ...
|
|
Revision tags: release/14.0.0 |
|
| #
031beb4e |
| 16-Aug-2023 |
Warner Losh <imp@FreeBSD.org> |
sys: Remove $FreeBSD$: one-line sh pattern
Remove /^\s*#[#!]?\s*\$FreeBSD\$.*$\n/
|
|
Revision tags: release/13.2.0, release/12.4.0, release/13.1.0, release/12.3.0 |
|
| #
828f2572 |
| 15-Sep-2021 |
John Baldwin <jhb@FreeBSD.org> |
Remove nonexistent include path for arm64 crypto files.
Reviewed by: emaste
Differential Revision: https://reviews.freebsd.org/D31932
|
|
Revision tags: release/13.0.0 |
|
| #
ed9b7f44 |
| 13-Jan-2021 |
Oleksandr Tymoshenko <gonzo@FreeBSD.org> |
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.
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 <andrew@FreeBSD.org> |
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 |
|
| #
1409e715 |
| 21-Aug-2017 |
Hans Petter Selasky <hselasky@FreeBSD.org> |
Merge ^/head r322398 through r322746.
|
| #
3e3648ce |
| 19-Aug-2017 |
Enji Cooper <ngie@FreeBSD.org> |
MFhead@r322698
|
| #
3f32b92b |
| 19-Aug-2017 |
Andrew Turner <andrew@FreeBSD.org> |
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 <ngie@FreeBSD.org> |
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
|
| #
0ed76ec8 |
| 24-Nov-2016 |
Dimitry Andric <dim@FreeBSD.org> |
Merge ^/head r308870 through r309105.
|
| #
d6699d29 |
| 21-Nov-2016 |
Andrew Turner <andrew@FreeBSD.org> |
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 ...
|