summaryrefslogtreecommitdiff
path: root/sys/crypto
diff options
context:
space:
mode:
authorjakllsch <jakllsch@NetBSD.org>2020-09-07 18:06:13 +0000
committerjakllsch <jakllsch@NetBSD.org>2020-09-07 18:06:13 +0000
commit4dae00f56efe8fc88eaff8dbe8ae340ed28fde5b (patch)
tree6a9ca367d7d45b8c62bd9624abd29ecb17879368 /sys/crypto
parent96000e664a037e99b4025a5176309855c53b80fd (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.h4
-rw-r--r--sys/crypto/chacha/arch/arm/arm_neon.h4
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