commit 7613b3d6b871a1dbd2b84eb51b14c6d45d9970ea
author Dave Rodgman <dave.rodgman@arm.com> Tue May 23 00:48:38 2023 +0100
committer Dave Rodgman <dave.rodgman@gmail.com> Tue May 23 08:16:01 2023 +0100
tree c607b5e063c569c2ae69be44b4cc713e8558d87a
parent 262d8ced795d72114c3bfdb0786ae8561ec3e266

Fix xor fail for large block size

Signed-off-by: Dave Rodgman <dave.rodgman@arm.com>

library/common.h

diff --git a/library/common.h b/library/common.h
index 9c09602..94b8c5d 100644
--- a/library/common.h
+++ b/library/common.h
@@ -131,10 +131,10 @@
 #if defined(MBEDTLS_EFFICIENT_UNALIGNED_ACCESS)
 #if defined(__aarch64__) && defined(__ARM_NEON)
     for (; (i + 16) <= n; i += 16) {
-        uint64x2_t v1 = vld1q_u64((uint64_t *) a);
-        uint64x2_t v2 = vld1q_u64((uint64_t *) b);
+        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, x);
+        vst1q_u64((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 */