vppinfra: add support for avx512 alignment version of load and store

Type: improvement

Signed-off-by: Zhiyong Yang <[email protected]>
Change-Id: Idfec9cb9370a8cf4966d3fdfa440496f21e17005

diff --git a/src/vppinfra/vector_avx512.h b/src/vppinfra/vector_avx512.h
index 0665a23..8a82650 100644 (file)
--- a/src/vppinfra/vector_avx512.h
+++ b/src/vppinfra/vector_avx512.h
@@ -35,6 +35,14 @@ t##s##x##c##_splat (t##s x)                                          \
 { return (t##s##x##c) _mm512_set1_##i (x); }                           \
 \
 static_always_inline t##s##x##c                                                \
+t##s##x##c##_load_aligned (void *p)                                    \
+{ return (t##s##x##c) _mm512_load_si512 (p); }                         \
+\
+static_always_inline void                                              \
+t##s##x##c##_store_aligned (t##s##x##c v, void *p)                     \
+{ _mm512_store_si512 ((__m512i *) p, (__m512i) v); }                   \
+\
+static_always_inline t##s##x##c                                                \
 t##s##x##c##_load_unaligned (void *p)                                  \
 { return (t##s##x##c) _mm512_loadu_si512 (p); }                                \
 \