X-Git-Url: https://gerrit.fd.io/r/gitweb?a=blobdiff_plain;ds=sidebyside;f=src%2Fvppinfra%2Fvector_avx512.h;h=6eb7c5eaa4d726127502f676150ef8d6ee8e2370;hb=f9c8fe41280a48f95216cab43eab8db00ee592e1;hp=8a82650e1e8d89237359d389a34fac95b00d7910;hpb=0c7aa7ab54dd6c9074079d589d0c32873a1085bb;p=vpp.git

diff --git a/src/vppinfra/vector_avx512.h b/src/vppinfra/vector_avx512.h
index 8a82650e1e8..6eb7c5eaa4d 100644
--- a/src/vppinfra/vector_avx512.h
+++ b/src/vppinfra/vector_avx512.h
@@ -191,6 +191,25 @@ u8x64_reflect_u8x16 (u8x64 x)
   return (u8x64) _mm512_shuffle_epi8 ((__m512i) x, (__m512i) mask);
 }
 
+static_always_inline u8x64
+u8x64_shuffle (u8x64 v, u8x64 m)
+{
+  return (u8x64) _mm512_shuffle_epi8 ((__m512i) v, (__m512i) m);
+}
+
+#define u8x64_align_right(a, b, imm) \
+  (u8x64) _mm512_alignr_epi8 ((__m512i) a, (__m512i) b, imm)
+
+static_always_inline u32
+u32x16_sum_elts (u32x16 sum16)
+{
+  u32x8 sum8;
+  sum16 += (u32x16) u8x64_align_right (sum16, sum16, 8);
+  sum16 += (u32x16) u8x64_align_right (sum16, sum16, 4);
+  sum8 = u32x16_extract_hi (sum16) + u32x16_extract_lo (sum16);
+  return sum8[0] + sum8[4];
+}
+
 static_always_inline u8x64
 u8x64_mask_load (u8x64 a, void *p, u64 mask)
 {