ARMmbed/mbedtls
1
0
Fork 0
mirror of https://github.com/ARMmbed/mbedtls.git synced 2025-06-25 22:56:35 +08:00
Code Issues Releases Wiki Activity

Fix xor fail for large block size

Browse Source 
Signed-off-by: Dave Rodgman <dave.rodgman@arm.com>
This commit is contained in:
Dave Rodgman 2023-05-23 00:48:38 +01:00 committed by Dave Rodgman
parent 262d8ced79
commit 7613b3d6b8
1 changed files with 3 additions and 3 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

6
library/common.h
View File

@ -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(MBEDTLS_EFFICIENT_UNALIGNED_ACCESS)
#if defined(__aarch64__) && defined(__ARM_NEON) #if defined(__aarch64__) && defined(__ARM_NEON)
for (; (i + 16) <= n; i += 16) { for (; (i + 16) <= n; i += 16) {
uint64x2_t v1 = vld1q_u64((uint64_t *) a); uint64x2_t v1 = vld1q_u64((uint64_t *) (a + i));
uint64x2_t v2 = vld1q_u64((uint64_t *) b); uint64x2_t v2 = vld1q_u64((uint64_t *) (b + i));
uint64x2_t x = veorq_u64(v1, v2); 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__) #elif defined(__amd64__) || defined(__x86_64__) || defined(__aarch64__)
/* This codepath probably only makes sense on architectures with 64-bit registers */ /* This codepath probably only makes sense on architectures with 64-bit registers */