summaryrefslogtreecommitdiffstats
path: root/vppinfra/vppinfra/memcpy_avx.h
diff options
context:
space:
mode:
Diffstat (limited to 'vppinfra/vppinfra/memcpy_avx.h')
-rw-r--r--vppinfra/vppinfra/memcpy_avx.h13
1 files changed, 5 insertions, 8 deletions
diff --git a/vppinfra/vppinfra/memcpy_avx.h b/vppinfra/vppinfra/memcpy_avx.h
index e987d044b58..e3feb76b6b7 100644
--- a/vppinfra/vppinfra/memcpy_avx.h
+++ b/vppinfra/vppinfra/memcpy_avx.h
@@ -51,22 +51,19 @@
#include <stdint.h>
#include <x86intrin.h>
+typedef u8 u8x16u __attribute__ ((vector_size (16), aligned (1)));
+typedef u8 u8x32u __attribute__ ((vector_size (32), aligned (1)));
+
static inline void
clib_mov16 (u8 * dst, const u8 * src)
{
- __m128i xmm0;
-
- xmm0 = _mm_loadu_si128 ((const __m128i *) src);
- _mm_storeu_si128 ((__m128i *) dst, xmm0);
+ *(u8x16u *) dst = *(u8x16u *) src;
}
static inline void
clib_mov32 (u8 * dst, const u8 * src)
{
- __m256i ymm0;
-
- ymm0 = _mm256_loadu_si256 ((const __m256i *) src);
- _mm256_storeu_si256 ((__m256i *) dst, ymm0);
+ *(u8x32u *) dst = *(u8x32u *) src;
}
static inline void