diff options
| author | jakllsch <jakllsch@NetBSD.org> | 2020-09-07 18:06:13 +0000 |
|---|---|---|
| committer | jakllsch <jakllsch@NetBSD.org> | 2020-09-07 18:06:13 +0000 |
| commit | 4dae00f56efe8fc88eaff8dbe8ae340ed28fde5b (patch) | |
| tree | 6a9ca367d7d45b8c62bd9624abd29ecb17879368 /sys/crypto | |
| parent | 96000e664a037e99b4025a5176309855c53b80fd (diff) | |
Fix vgetq_lane_u32 for aarch64eb with GCC
Fixes NEON AES on aarch64eb
Diffstat (limited to 'sys/crypto')
| -rw-r--r-- | sys/crypto/aes/arch/arm/arm_neon.h | 4 | ||||
| -rw-r--r-- | sys/crypto/chacha/arch/arm/arm_neon.h | 4 |
2 files changed, 4 insertions, 4 deletions
diff --git a/sys/crypto/aes/arch/arm/arm_neon.h b/sys/crypto/aes/arch/arm/arm_neon.h index ef54e71c318..3d9a0064a02 100644 --- a/sys/crypto/aes/arch/arm/arm_neon.h +++ b/sys/crypto/aes/arch/arm/arm_neon.h @@ -1,4 +1,4 @@ -/* $NetBSD: arm_neon.h,v 1.10 2020/08/09 02:49:38 riastradh Exp $ */ +/* $NetBSD: arm_neon.h,v 1.11 2020/09/07 18:06:13 jakllsch Exp $ */ /*- * Copyright (c) 2020 The NetBSD Foundation, Inc. @@ -232,7 +232,7 @@ static __inline uint32_t vgetq_lane_u32(uint32x4_t __v, uint8_t __i) { #ifdef __aarch64__ - return __v[__i]; + return __v[__neon_laneq_index(__v,__i)]; #else return (uint32_t)__builtin_neon_vget_laneuv4si((int32x4_t)__v, __i); #endif diff --git a/sys/crypto/chacha/arch/arm/arm_neon.h b/sys/crypto/chacha/arch/arm/arm_neon.h index 39d8af9d07b..7ca77398486 100644 --- a/sys/crypto/chacha/arch/arm/arm_neon.h +++ b/sys/crypto/chacha/arch/arm/arm_neon.h @@ -1,4 +1,4 @@ -/* $NetBSD: arm_neon.h,v 1.6 2020/08/09 02:49:38 riastradh Exp $ */ +/* $NetBSD: arm_neon.h,v 1.7 2020/09/07 18:06:13 jakllsch Exp $ */ /*- * Copyright (c) 2020 The NetBSD Foundation, Inc. @@ -232,7 +232,7 @@ static __inline uint32_t vgetq_lane_u32(uint32x4_t __v, uint8_t __i) { #ifdef __aarch64__ - return __v[__i]; + return __v[__neon_laneq_index(__v, __i)]; #else return (uint32_t)__builtin_neon_vget_laneuv4si((int32x4_t)__v, __i); #endif |
