src/sys/modules/armv8crypto, branch releng/12.1 FreeBSD source tree https://cgit-dev.freebsd.org/src/atom?h=releng%2F12.1 2018-07-16T15:39:33Z Create an empty stdint.h for arm_neon.h to include. 2018-07-16T15:39:33Z Andrew Turner andrew@FreeBSD.org 2018-07-16T15:39:33Z urn:sha1:a9dc38def44742322a94bce24a34755bb8b7754f 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 Use armv8-a in -march, it is accepted by both clang and gcc. 2017-08-19T17:15:40Z Andrew Turner andrew@FreeBSD.org 2017-08-19T17:15:40Z urn:sha1:3f32b92b1d0632debfc20ecec7e8f3dd181c0030 Sponsored by: DARPA, AFRL sys/modules: normalize .CURDIR-relative paths to SRCTOP 2017-03-04T10:10:17Z Enji Cooper ngie@FreeBSD.org 2017-03-04T10:10:17Z urn:sha1:193d9e768ba63fcfb187cfd17f461f7d41345048 This simplifies make output/logic Tested with: `cd sys/modules; make ALL_MODULES=` on amd64 MFC after: 1 month Sponsored by: Dell EMC Isilon Add accelerated AES with using the ARMv8 crypto instructions. This is based 2016-11-21T11:18:00Z Andrew Turner andrew@FreeBSD.org 2016-11-21T11:18:00Z urn:sha1:d6699d292b1bbb62118c5316fcec666fa186276d 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