From 2070c2074eb33271e86efc31c9861e967d4a59ac Mon Sep 17 00:00:00 2001 From: Dave Rodgman Date: Wed, 7 Jun 2023 16:25:58 +0100 Subject: [PATCH] Avoid possible NEON alignment issue Signed-off-by: Dave Rodgman --- library/common.h | 8 ++++---- 1 file changed, 4 insertions(+), 4 deletions(-) diff --git a/library/common.h b/library/common.h index ac6883ce1..7e21a0c34 100644 --- a/library/common.h +++ b/library/common.h @@ -131,10 +131,10 @@ inline void mbedtls_xor(unsigned char *r, const unsigned char *a, const unsigned #if defined(MBEDTLS_EFFICIENT_UNALIGNED_ACCESS) #if defined(__ARM_NEON) for (; (i + 16) <= n; i += 16) { - uint64x2_t v1 = vld1q_u64((uint64_t *) (a + i)); - uint64x2_t v2 = vld1q_u64((uint64_t *) (b + i)); - uint64x2_t x = veorq_u64(v1, v2); - vst1q_u64((uint64_t *) (r + i), x); + uint8x16_t v1 = vld1q_u8((uint64_t *) (a + i)); + uint8x16_t v2 = vld1q_u8((uint64_t *) (b + i)); + uint8x16_t x = veorq_u8(v1, v2); + vst1q_u8((uint64_t *) (r + i), x); } #elif defined(__amd64__) || defined(__x86_64__) || defined(__aarch64__) /* This codepath probably only makes sense on architectures with 64-bit registers */