yuzu-emu/mbedtls
2
0
Fork 0
Code Issues Pull requests Projects Releases Packages Wiki Activity

Avoid possible NEON alignment issue

Browse source 
Signed-off-by: Dave Rodgman <dave.rodgman@arm.com>
This commit is contained in:
Dave Rodgman 2023-06-07 16:25:58 +01:00
parent 9d1635e742
commit 2070c2074e
1 changed files with 4 additions and 4 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

8
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(__ARM_NEON) #if defined(__ARM_NEON)
for (; (i + 16) <= n; i += 16) { for (; (i + 16) <= n; i += 16) {
uint64x2_t v1 = vld1q_u64((uint64_t *) (a + i)); uint8x16_t v1 = vld1q_u8((uint64_t *) (a + i));
uint64x2_t v2 = vld1q_u64((uint64_t *) (b + i)); uint8x16_t v2 = vld1q_u8((uint64_t *) (b + i));
uint64x2_t x = veorq_u64(v1, v2); uint8x16_t x = veorq_u8(v1, v2);
vst1q_u64((uint64_t *) (r + i), x); vst1q_u8((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 */