Home
last modified time | relevance | path

Searched refs:index_array (Results 1 – 5 of 5) sorted by relevance

/f-stack/dpdk/lib/librte_acl/
H A Dacl_run_altivec.h225 (xmm_t *)&index_array[0], (xmm_t *)&index_array[2]); in search_altivec_8()
227 (xmm_t *)&index_array[4], (xmm_t *)&index_array[6]); in search_altivec_8()
230 (xmm_t *)&index_array[0], (xmm_t *)&index_array[2]); in search_altivec_8()
232 (xmm_t *)&index_array[4], (xmm_t *)&index_array[6]); in search_altivec_8()
235 (xmm_t *)&index_array[0], (xmm_t *)&index_array[2]); in search_altivec_8()
237 (xmm_t *)&index_array[4], (xmm_t *)&index_array[6]); in search_altivec_8()
240 (xmm_t *)&index_array[0], (xmm_t *)&index_array[2]); in search_altivec_8()
242 (xmm_t *)&index_array[4], (xmm_t *)&index_array[6]); in search_altivec_8()
289 (xmm_t *)&index_array[0], (xmm_t *)&index_array[2]); in search_altivec_4()
291 (xmm_t *)&index_array[0], (xmm_t *)&index_array[2]); in search_altivec_4()
[all …]
H A Dacl_run_neon.h165 uint64_t index_array[8]; in search_neon_8() local
179 acl_match_check_x4(0, ctx, parms, &flows, &index_array[0]); in search_neon_8()
180 acl_match_check_x4(4, ctx, parms, &flows, &index_array[4]); in search_neon_8()
198 input0 = transition4(input0, flows.trans, &index_array[0]); in search_neon_8()
227 uint64_t index_array[4]; in search_neon_4() local
241 acl_match_check_x4(0, ctx, parms, &flows, index_array); in search_neon_4()
251 input = transition4(input, flows.trans, index_array); in search_neon_4()
252 input = transition4(input, flows.trans, index_array); in search_neon_4()
253 input = transition4(input, flows.trans, index_array); in search_neon_4()
254 input = transition4(input, flows.trans, index_array); in search_neon_4()
[all …]
H A Dacl_run_avx2.h165 uint64_t index_array[MAX_SEARCHES_AVX16]; in search_avx2x16() local
176 index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); in search_avx2x16()
179 t0 = _mm256_set_epi64x(index_array[5], index_array[4], in search_avx2x16()
180 index_array[1], index_array[0]); in search_avx2x16()
181 t1 = _mm256_set_epi64x(index_array[7], index_array[6], in search_avx2x16()
182 index_array[3], index_array[2]); in search_avx2x16()
186 t0 = _mm256_set_epi64x(index_array[13], index_array[12], in search_avx2x16()
187 index_array[9], index_array[8]); in search_avx2x16()
188 t1 = _mm256_set_epi64x(index_array[15], index_array[14], in search_avx2x16()
189 index_array[11], index_array[10]); in search_avx2x16()
H A Dacl_run_sse.h199 uint64_t index_array[MAX_SEARCHES_SSE8]; in search_sse_8() local
210 index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); in search_sse_8()
220 indices1 = _mm_loadu_si128((xmm_t *) &index_array[0]); in search_sse_8()
221 indices2 = _mm_loadu_si128((xmm_t *) &index_array[2]); in search_sse_8()
223 indices3 = _mm_loadu_si128((xmm_t *) &index_array[4]); in search_sse_8()
224 indices4 = _mm_loadu_si128((xmm_t *) &index_array[6]); in search_sse_8()
288 uint64_t index_array[MAX_SEARCHES_SSE4]; in search_sse_4() local
298 index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); in search_sse_4()
301 indices1 = _mm_loadu_si128((xmm_t *) &index_array[0]); in search_sse_4()
302 indices2 = _mm_loadu_si128((xmm_t *) &index_array[2]); in search_sse_4()
H A Dacl_run_scalar.c117 uint64_t index_array[MAX_SEARCHES_SCALAR]; in rte_acl_classify_scalar() local
126 index_array[n] = acl_start_next_trie(&flows, parms, n, ctx); in rte_acl_classify_scalar()
129 transition0 = index_array[0]; in rte_acl_classify_scalar()
130 transition1 = index_array[1]; in rte_acl_classify_scalar()