git.droids-corp.org
/
dpdk.git
/ blobdiff
commit
grep
author
committer
pickaxe
?
search:
re
summary
|
shortlog
|
log
|
commit
|
commitdiff
|
tree
raw
|
inline
| side by side
ipc: end multiprocess thread during cleanup
[dpdk.git]
/
lib
/
acl
/
acl_run_avx512x16.h
diff --git
a/lib/acl/acl_run_avx512x16.h
b/lib/acl/acl_run_avx512x16.h
index
da244bc
..
f87293e
100644
(file)
--- a/
lib/acl/acl_run_avx512x16.h
+++ b/
lib/acl/acl_run_avx512x16.h
@@
-10,7
+10,7
@@
*/
/*
*/
/*
- * This implementation uses 512-bit registers(zmm) and in
strinct
s.
+ * This implementation uses 512-bit registers(zmm) and in
trinsic
s.
* So our main SIMD type is 512-bit width and each such variable can
* process sizeof(__m512i) / sizeof(uint32_t) == 16 entries in parallel.
*/
* So our main SIMD type is 512-bit width and each such variable can
* process sizeof(__m512i) / sizeof(uint32_t) == 16 entries in parallel.
*/
@@
-25,20
+25,20
@@
#define _F_(x) x##_avx512x16
/*
#define _F_(x) x##_avx512x16
/*
- * Same in
strincts have different syntaxi
s (depending on the bit-width),
+ * Same in
trinsics have different syntaxe
s (depending on the bit-width),
* so to overcome that few macros need to be defined.
*/
* so to overcome that few macros need to be defined.
*/
-/* Naming convention for generic epi(packed integers) type in
strinct
s. */
+/* Naming convention for generic epi(packed integers) type in
trinsic
s. */
#define _M_I_(x) _mm512_##x
#define _M_I_(x) _mm512_##x
-/* Naming convention for si(whole simd integer) type in
strinct
s. */
+/* Naming convention for si(whole simd integer) type in
trinsic
s. */
#define _M_SI_(x) _mm512_##x##_si512
#define _M_SI_(x) _mm512_##x##_si512
-/* Naming convention for masked gather type in
strinct
s. */
+/* Naming convention for masked gather type in
trinsic
s. */
#define _M_MGI_(x) _mm512_##x
#define _M_MGI_(x) _mm512_##x
-/* Naming convention for gather type in
strinct
s. */
+/* Naming convention for gather type in
trinsic
s. */
#define _M_GI_(name, idx, base, scale) _mm512_##name(idx, base, scale)
/* num/mask of transitions per SIMD regs */
#define _M_GI_(name, idx, base, scale) _mm512_##name(idx, base, scale)
/* num/mask of transitions per SIMD regs */
@@
-239,7
+239,7
@@
_F_(gather_bytes)(__m512i zero, const __m512i p[2], const uint32_t m[2],
}
/*
}
/*
- * Resolve matches for multiple categories (GT 8, use 512b instuctions/regs)
+ * Resolve matches for multiple categories (GT 8, use 512b inst
r
uctions/regs)
*/
static inline void
resolve_mcgt8_avx512x1(uint32_t result[],
*/
static inline void
resolve_mcgt8_avx512x1(uint32_t result[],
@@
-252,8
+252,6
@@
resolve_mcgt8_avx512x1(uint32_t result[],
__mmask16 cm, sm;
__m512i cp, cr, np, nr;
__mmask16 cm, sm;
__m512i cp, cr, np, nr;
- const uint32_t match_log = 5;
-
res = pr->results;
pri = pr->priority;
res = pr->results;
pri = pr->priority;
@@
-261,7
+259,7
@@
resolve_mcgt8_avx512x1(uint32_t result[],
for (k = 0; k != nb_pkt; k++, result += nb_cat) {
for (k = 0; k != nb_pkt; k++, result += nb_cat) {
- mi = match[k] <<
match_log
;
+ mi = match[k] <<
ACL_MATCH_LOG
;
cr = _mm512_maskz_loadu_epi32(cm, res + mi);
cp = _mm512_maskz_loadu_epi32(cm, pri + mi);
cr = _mm512_maskz_loadu_epi32(cm, res + mi);
cp = _mm512_maskz_loadu_epi32(cm, pri + mi);
@@
-269,7
+267,7
@@
resolve_mcgt8_avx512x1(uint32_t result[],
for (i = 1, pm = match + nb_pkt; i != nb_trie;
i++, pm += nb_pkt) {
for (i = 1, pm = match + nb_pkt; i != nb_trie;
i++, pm += nb_pkt) {
- mi = pm[k] <<
match_log
;
+ mi = pm[k] <<
ACL_MATCH_LOG
;
nr = _mm512_maskz_loadu_epi32(cm, res + mi);
np = _mm512_maskz_loadu_epi32(cm, pri + mi);
nr = _mm512_maskz_loadu_epi32(cm, res + mi);
np = _mm512_maskz_loadu_epi32(cm, pri + mi);