From 31d270db5b5d8fa660fa498cdeecdd20b09e4462 Mon Sep 17 00:00:00 2001 From: Anton Khirnov Date: Wed, 30 Nov 2022 13:11:46 +0100 Subject: SSE/AVX: always use unaligned loads --- src/vectors-8-AVX.h | 2 +- src/vectors-8-SSE2.h | 2 +- 2 files changed, 2 insertions(+), 2 deletions(-) diff --git a/src/vectors-8-AVX.h b/src/vectors-8-AVX.h index 52319b3..b3e31ec 100644 --- a/src/vectors-8-AVX.h +++ b/src/vectors-8-AVX.h @@ -116,7 +116,7 @@ CCTK_BOOLEAN8 vec8_eltb(CCTK_BOOLEAN8_VEC const x, std::ptrdiff_t const d) static inline CCTK_ATTRIBUTE_ALWAYS_INLINE CCTK_REAL8_VEC vec8_load(CCTK_REAL8 const& p) { - return _mm256_load_pd(&p); + return _mm256_loadu_pd(&p); } static inline CCTK_ATTRIBUTE_ALWAYS_INLINE CCTK_REAL8_VEC vec8_loadu(CCTK_REAL8 const& p) diff --git a/src/vectors-8-SSE2.h b/src/vectors-8-SSE2.h index b6dcfa6..f8a96dc 100644 --- a/src/vectors-8-SSE2.h +++ b/src/vectors-8-SSE2.h @@ -161,7 +161,7 @@ CCTK_BOOLEAN8 vec8_eltb(CCTK_BOOLEAN8_VEC const x, std::ptrdiff_t const d) static inline CCTK_ATTRIBUTE_ALWAYS_INLINE CCTK_REAL8_VEC vec8_load(CCTK_REAL8 const& p) { - return _mm_load_pd(&p); + return _mm_loadu_pd(&p); } static inline CCTK_ATTRIBUTE_ALWAYS_INLINE CCTK_REAL8_VEC vec8_loadu(CCTK_REAL8 const& p) -- cgit v1.2.3