Home
last modified time | relevance | path

Searched refs:results (Results 1 – 25 of 77) sorted by relevance

1234

/dpdk/drivers/net/fm10k/base/
H A Dfm10k_tlv.c507 if (!attr || !results) in fm10k_tlv_attr_parse()
512 results[i] = NULL; in fm10k_tlv_attr_parse()
523 results[0] = attr; in fm10k_tlv_attr_parse()
543 results[attr_id] = attr; in fm10k_tlv_attr_parse()
576 u32 *results[FM10K_TLV_RESULTS_MAX]; in fm10k_tlv_msg_parse() local
607 return data->func(hw, results, mbx); in fm10k_tlv_msg_parse()
771 results[FM10K_TEST_MSG_STRING], in fm10k_tlv_msg_test()
789 if (!!results[FM10K_TEST_MSG_U8]) { in fm10k_tlv_msg_test()
797 if (!!results[FM10K_TEST_MSG_U16]) { in fm10k_tlv_msg_test()
821 if (!!results[FM10K_TEST_MSG_S8]) { in fm10k_tlv_msg_test()
[all …]
H A Dfm10k_pf.c1201 UNREFERENCED_1PARAMETER(results); in fm10k_iov_msg_msix_pf()
1252 if (!err && !!results[FM10K_MAC_VLAN_MSG_VLAN]) { in fm10k_iov_msg_mac_vlan_pf()
1253 result = results[FM10K_MAC_VLAN_MSG_VLAN]; in fm10k_iov_msg_mac_vlan_pf()
1291 if (!err && !!results[FM10K_MAC_VLAN_MSG_MAC]) { in fm10k_iov_msg_mac_vlan_pf()
1292 result = results[FM10K_MAC_VLAN_MSG_MAC]; in fm10k_iov_msg_mac_vlan_pf()
1318 if (!err && !!results[FM10K_MAC_VLAN_MSG_MULTICAST]) { in fm10k_iov_msg_mac_vlan_pf()
1319 result = results[FM10K_MAC_VLAN_MSG_MULTICAST]; in fm10k_iov_msg_mac_vlan_pf()
1411 if (!!results[FM10K_LPORT_STATE_MSG_XCAST_MODE]) { in fm10k_iov_msg_lport_state_pf()
1412 result = results[FM10K_LPORT_STATE_MSG_XCAST_MODE]; in fm10k_iov_msg_lport_state_pf()
1428 } else if (!results[FM10K_LPORT_STATE_MSG_DISABLE]) { in fm10k_iov_msg_lport_state_pf()
[all …]
H A Dfm10k_vf.c225 s32 fm10k_msg_mac_vlan_vf(struct fm10k_hw *hw, u32 **results, in fm10k_msg_mac_vlan_vf() argument
237 results[FM10K_MAC_VLAN_MSG_DEFAULT_MAC], in fm10k_msg_mac_vlan_vf()
413 s32 fm10k_msg_lport_state_vf(struct fm10k_hw *hw, u32 **results, in fm10k_msg_lport_state_vf() argument
419 hw->mac.dglort_map = !results[FM10K_LPORT_STATE_MSG_READY] ? in fm10k_msg_lport_state_vf()
/dpdk/lib/acl/
H A Dacl_run_avx512.c80 res = pr->results; in resolve_mcle8_avx512x1()
114 uint32_t *results, uint32_t num, uint32_t categories) in rte_acl_classify_avx512x16() argument
120 search_avx512x8x2(ctx, data, results, max_iter, categories); in rte_acl_classify_avx512x16()
122 results += max_iter * categories; in rte_acl_classify_avx512x16()
130 return search_sse_8(ctx, data, results, num, categories); in rte_acl_classify_avx512x16()
132 return search_sse_4(ctx, data, results, num, categories); in rte_acl_classify_avx512x16()
141 uint32_t *results, uint32_t num, uint32_t categories) in rte_acl_classify_avx512x32() argument
147 search_avx512x16x2(ctx, data, results, max_iter, categories); in rte_acl_classify_avx512x32()
149 results += max_iter * categories; in rte_acl_classify_avx512x32()
159 return search_sse_8(ctx, data, results, num, categories); in rte_acl_classify_avx512x32()
[all …]
H A Dacl_run_scalar.c23 const uint32_t *results; in resolve_priority_scalar() local
25 saved_results = parms[n].cmplt->results; in resolve_priority_scalar()
29 results = p[transition].results; in resolve_priority_scalar()
38 saved_results[i] = results[i]; in resolve_priority_scalar()
42 saved_results[i + 1] = results[i + 1]; in resolve_priority_scalar()
46 saved_results[i + 2] = results[i + 2]; in resolve_priority_scalar()
50 saved_results[i + 3] = results[i + 3]; in resolve_priority_scalar()
60 saved_results[i] = results[i]; in resolve_priority_scalar()
61 saved_results[i + 1] = results[i + 1]; in resolve_priority_scalar()
62 saved_results[i + 2] = results[i + 2]; in resolve_priority_scalar()
[all …]
H A Dacl_run.h49 uint32_t *results; member
59 uint32_t *results; /* running results. */ member
87 uint32_t *results) in alloc_completion() argument
97 p[n].results = results; in alloc_completion()
119 parms[n].cmplt->results[0] = p[transition].results[0]; in resolve_single_priority()
142 flows->results + in acl_start_next_trie()
176 uint32_t cmplt_size, const uint8_t **data, uint32_t *results, in acl_set_flow() argument
188 flows->results = results; in acl_set_flow()
H A Dacl.h96 int results[RTE_ACL_MAX_CATEGORIES]; member
100 uint32_t results[RTE_ACL_MAX_CATEGORIES]; member
202 uint32_t *results, uint32_t num, uint32_t categories);
206 uint32_t *results, uint32_t num, uint32_t categories);
210 uint32_t *results, uint32_t num, uint32_t categories);
214 uint32_t *results, uint32_t num, uint32_t categories);
218 uint32_t *results, uint32_t num, uint32_t categories);
222 uint32_t *results, uint32_t num, uint32_t categories);
226 uint32_t *results, uint32_t num, uint32_t categories);
H A Dacl_run_avx2.c14 uint32_t *results, uint32_t num, uint32_t categories) in rte_acl_classify_avx2() argument
17 return search_avx2x16(ctx, data, results, num, categories); in rte_acl_classify_avx2()
19 return search_sse_8(ctx, data, results, num, categories); in rte_acl_classify_avx2()
21 return search_sse_4(ctx, data, results, num, categories); in rte_acl_classify_avx2()
23 return rte_acl_classify_scalar(ctx, data, results, num, in rte_acl_classify_avx2()
H A Dacl_run_neon.c9 uint32_t *results, uint32_t num, uint32_t categories) in rte_acl_classify_neon() argument
12 return search_neon_8(ctx, data, results, num, categories); in rte_acl_classify_neon()
14 return search_neon_4(ctx, data, results, num, categories); in rte_acl_classify_neon()
16 return rte_acl_classify_scalar(ctx, data, results, num, in rte_acl_classify_neon()
H A Dacl_run_sse.c9 uint32_t *results, uint32_t num, uint32_t categories) in rte_acl_classify_sse() argument
12 return search_sse_8(ctx, data, results, num, categories); in rte_acl_classify_sse()
14 return search_sse_4(ctx, data, results, num, categories); in rte_acl_classify_sse()
16 return rte_acl_classify_scalar(ctx, data, results, num, in rte_acl_classify_sse()
H A Dacl_run_altivec.c10 uint32_t *results, uint32_t num, uint32_t categories) in rte_acl_classify_altivec() argument
13 return search_altivec_8(ctx, data, results, num, categories); in rte_acl_classify_altivec()
15 return search_altivec_4(ctx, data, results, num, categories); in rte_acl_classify_altivec()
17 return rte_acl_classify_scalar(ctx, data, results, num, in rte_acl_classify_altivec()
H A Dacl_run_neon.h39 int32x4_t results, priority, results1, priority1; in resolve_priority_neon() local
44 saved_results = (int32_t *)(&parms[n].cmplt->results[x]); in resolve_priority_neon()
48 results = vld1q_s32( in resolve_priority_neon()
49 (const int32_t *)&p[transition].results[x]); in resolve_priority_neon()
61 results = vbslq_s32(selector, results1, results); in resolve_priority_neon()
66 vst1q_s32(saved_results, results); in resolve_priority_neon()
161 uint32_t *results, uint32_t total_packets, uint32_t categories) in search_neon_8() argument
170 acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, in search_neon_8()
223 uint32_t *results, int total_packets, uint32_t categories) in search_neon_4() argument
232 acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, in search_neon_4()
H A Dacl_run_sse.h60 xmm_t results, priority, results1, priority1, selector; in resolve_priority_sse() local
65 saved_results = (xmm_t *)(&parms[n].cmplt->results[x]); in resolve_priority_sse()
70 results = _mm_loadu_si128( in resolve_priority_sse()
71 (const xmm_t *)&p[transition].results[x]); in resolve_priority_sse()
84 results = _mm_blendv_epi8(results, results1, selector); in resolve_priority_sse()
90 _mm_storeu_si128(saved_results, results); in resolve_priority_sse()
195 uint32_t *results, uint32_t total_packets, uint32_t categories) in search_sse_8() argument
205 acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, in search_sse_8()
284 uint32_t *results, int total_packets, uint32_t categories) in search_sse_4() argument
293 acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, in search_sse_4()
H A Dacl_run_altivec.h43 xmm_t results, priority, results1, priority1; in resolve_priority_altivec() local
49 saved_results = (xmm_t *)(&parms[n].cmplt->results[x]); in resolve_priority_altivec()
54 results = *(const xmm_t *)&p[transition].results[x]; in resolve_priority_altivec()
66 results = vec_sel(results, results1, selector); in resolve_priority_altivec()
72 *saved_results = results; in resolve_priority_altivec()
188 uint32_t *results, uint32_t total_packets, uint32_t categories) in search_altivec_8() argument
197 acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, in search_altivec_8()
259 uint32_t *results, int total_packets, uint32_t categories) in search_altivec_4() argument
268 acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, in search_altivec_4()
H A Drte_acl.c27 __rte_unused uint32_t *results, in EAL_REGISTER_TAILQ()
37 __rte_unused uint32_t *results, in rte_acl_classify_avx512x32() argument
53 __rte_unused uint32_t *results, in rte_acl_classify_avx2() argument
65 __rte_unused uint32_t *results, in rte_acl_classify_sse() argument
77 __rte_unused uint32_t *results, in rte_acl_classify_neon() argument
89 __rte_unused uint32_t *results, in rte_acl_classify_altivec() argument
291 uint32_t *results, uint32_t num, uint32_t categories, in rte_acl_classify_alg() argument
298 return classify_fns[alg](ctx, data, results, num, categories); in rte_acl_classify_alg()
303 uint32_t *results, uint32_t num, uint32_t categories) in rte_acl_classify() argument
305 return rte_acl_classify_alg(ctx, data, results, num, categories, in rte_acl_classify()
H A Dacl_run_avx512x16.h255 res = pr->results; in resolve_mcgt8_avx512x1()
292 uint32_t *results, uint32_t total_packets, uint32_t categories) in search_avx512x16x2() argument
313 _F_(resolve_single_cat)(results, pr, match, total_packets, in search_avx512x16x2()
316 resolve_mcle8_avx512x1(results, pr, match, total_packets, in search_avx512x16x2()
319 resolve_mcgt8_avx512x1(results, pr, match, total_packets, in search_avx512x16x2()
H A Dacl_run_avx512x8.h209 uint32_t *results, uint32_t total_packets, uint32_t categories) in search_avx512x8x2() argument
230 _F_(resolve_single_cat)(results, pr, match, total_packets, in search_avx512x8x2()
233 resolve_mcle8_avx512x1(results, pr, match, total_packets, in search_avx512x8x2()
H A Drte_acl.h280 uint32_t *results, uint32_t num,
320 uint32_t *results, uint32_t num,
H A Dacl_run_avx2.h161 uint32_t *results, uint32_t total_packets, uint32_t categories) in search_avx2x16() argument
171 acl_set_flow(&flows, cmplt, RTE_DIM(cmplt), data, results, in search_avx2x16()
/dpdk/app/test/
H A Dtest_acl.c287 uint32_t results[dim * RTE_ACL_MAX_CATEGORIES]; in test_classify_alg() local
299 ret = rte_acl_classify(acx, data, results, in test_classify_alg()
547 uint32_t results[RTE_DIM(test_data)]; in test_build_ports_range() local
572 ret = rte_acl_classify(acx, data, results, in test_build_ports_range()
581 for (j = 0; j != RTE_DIM(results); j++) { in test_build_ports_range()
582 if (results[j] != test_data[j].allow) { in test_build_ports_range()
586 results[j]); in test_build_ports_range()
1078 ret = rte_acl_classify_alg(acx, data, results, in test_invalid_layout()
1090 __LINE__, i, results[i], in test_invalid_layout()
1097 ret = rte_acl_classify_alg(acx, data, results, RTE_DIM(results), 1, in test_invalid_layout()
[all …]
/dpdk/doc/guides/prog_guide/
H A Dpacket_classif_access_ctrl.rst520 rte_acl_classify(acx, data, results, 1, 4);
522 then the results[] array contains:
526 results[4] = {2, 3, 0, 0};
529 therefore results[0] contains the userdata for rule 2.
534 * For categories 2 and 3, there are no matches, so results[2] and results[3] contain zero,
544 rte_acl_classify(acx, data, results, 1, 4);
546 the results[] array contains:
550 results[4] = {1, 1, 0, 0};
562 rte_acl_classify(acx, data, results, 1, 4);
564 the results[] array contains:
[all …]
/dpdk/drivers/net/qede/
H A Dqede_debug.h412 struct dbg_attn_block_result *results);
426 struct dbg_attn_block_result *results);
757 struct dbg_attn_block_result *results);
/dpdk/doc/guides/tools/
H A Dtestregex.rst35 * Matching results (rule id, position, length), for each job.
37 * Matching results in absolute location (rule id, position , length),
/dpdk/drivers/crypto/mvsam/
H A Drte_mrvl_pmd.c1001 struct sam_cio_op_result results[nb_ops]; in mrvl_crypto_pmd_dequeue_burst() local
1005 ret = sam_cio_deq(cio, results, &nb_ops); in mrvl_crypto_pmd_dequeue_burst()
1018 ops[i] = results[i].cookie; in mrvl_crypto_pmd_dequeue_burst()
1020 switch (results[i].status) { in mrvl_crypto_pmd_dequeue_burst()
1030 dst->pkt_len = results[i].out_len; in mrvl_crypto_pmd_dequeue_burst()
1031 dst->data_len = results[i].out_len; in mrvl_crypto_pmd_dequeue_burst()
1040 "CIO returned Error: %d.", results[i].status); in mrvl_crypto_pmd_dequeue_burst()
/dpdk/drivers/net/qede/base/
H A Decore_dcbx.h24 struct ecore_dcbx_results results; member

1234