Home
last modified time | relevance | path

Searched refs:priority (Results 1 – 25 of 308) sorted by relevance

12345678910>>...13

/dpdk/app/test/
H A Dtest_acl.h84 .priority = 1},
90 .priority = 1},
97 .priority = 1},
103 .priority = 1},
110 .priority = 1},
116 .priority = 1},
371 .priority = 1},
678 .priority = 500
687 .priority = 400
696 .priority = 300
[all …]
H A Dtest_event_timer_adapter.c442 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_state()
499 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _arm_timers()
613 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _arm_timers_burst()
696 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_cancel_periodic()
738 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_cancel()
780 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _cancel_producer()
819 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _cancel_producer_burst()
1000 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_cancel_random()
1186 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in stat_inc_reset_ev_enq()
1279 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in event_timer_arm()
[all …]
/dpdk/lib/acl/
H A Dacl_run_scalar.c22 const int32_t *priority; in resolve_priority_scalar() local
26 saved_priority = parms[n].cmplt->priority; in resolve_priority_scalar()
30 priority = p[transition].priority; in resolve_priority_scalar()
36 if (saved_priority[i] <= priority[i]) { in resolve_priority_scalar()
37 saved_priority[i] = priority[i]; in resolve_priority_scalar()
41 saved_priority[i + 1] = priority[i + 1]; in resolve_priority_scalar()
45 saved_priority[i + 2] = priority[i + 2]; in resolve_priority_scalar()
55 saved_priority[i] = priority[i]; in resolve_priority_scalar()
56 saved_priority[i + 1] = priority[i + 1]; in resolve_priority_scalar()
57 saved_priority[i + 2] = priority[i + 2]; in resolve_priority_scalar()
[all …]
H A Dacl_run_neon.h39 int32x4_t results, priority, results1, priority1; in resolve_priority_neon() local
45 saved_priority = (int32_t *)(&parms[n].cmplt->priority[x]); in resolve_priority_neon()
50 priority = vld1q_s32( in resolve_priority_neon()
51 (const int32_t *)&p[transition].priority[x]); in resolve_priority_neon()
60 selector = vcgtq_s32(priority1, priority); in resolve_priority_neon()
62 priority = vbslq_s32(selector, priority1, priority); in resolve_priority_neon()
67 vst1q_s32(saved_priority, priority); in resolve_priority_neon()
H A Dacl_run_sse.h60 xmm_t results, priority, results1, priority1, selector; in resolve_priority_sse() local
67 (xmm_t *)(&parms[n].cmplt->priority[x]); in resolve_priority_sse()
72 priority = _mm_loadu_si128( in resolve_priority_sse()
73 (const xmm_t *)&p[transition].priority[x]); in resolve_priority_sse()
83 selector = _mm_cmpgt_epi32(priority1, priority); in resolve_priority_sse()
85 priority = _mm_blendv_epi8(priority, priority1, in resolve_priority_sse()
91 _mm_storeu_si128(saved_priority, priority); in resolve_priority_sse()
H A Dacl_run_altivec.h43 xmm_t results, priority, results1, priority1; in resolve_priority_altivec() local
51 (xmm_t *)(&parms[n].cmplt->priority[x]); in resolve_priority_altivec()
55 priority = *(const xmm_t *)&p[transition].priority[x]; in resolve_priority_altivec()
65 selector = vec_cmpgt(priority1, priority); in resolve_priority_altivec()
67 priority = vec_sel(priority, priority1, in resolve_priority_altivec()
73 *saved_priority = priority; in resolve_priority_altivec()
H A Dacl_run.h60 int32_t priority[RTE_ACL_MAX_CATEGORIES]; /* running priorities. */ member
115 parms[n].cmplt->priority[0] <= in resolve_single_priority()
116 p[transition].priority[0]) { in resolve_single_priority()
118 parms[n].cmplt->priority[0] = p[transition].priority[0]; in resolve_single_priority()
/dpdk/drivers/bus/fslmc/mc/
H A Ddpdmai.c327 uint8_t priority, in dpdmai_set_rx_queue() argument
339 cmd_params->dest_priority = cfg->dest_cfg.priority; in dpdmai_set_rx_queue()
340 cmd_params->priority = priority; in dpdmai_set_rx_queue()
369 uint8_t priority, in dpdmai_get_rx_queue() argument
382 cmd_params->priority = priority; in dpdmai_get_rx_queue()
395 attr->dest_cfg.priority = le32_to_cpu(rsp_params->dest_priority); in dpdmai_get_rx_queue()
419 uint8_t priority, in dpdmai_get_tx_queue() argument
432 cmd_params->priority = priority; in dpdmai_get_tx_queue()
H A Ddpci.c321 uint8_t priority, in dpci_set_rx_queue() argument
333 cmd_params->dest_priority = cfg->dest_cfg.priority; in dpci_set_rx_queue()
334 cmd_params->priority = priority; in dpci_set_rx_queue()
362 uint8_t priority, in dpci_get_rx_queue() argument
375 cmd_params->priority = priority; in dpci_get_rx_queue()
387 attr->dest_cfg.priority = rsp_params->dest_priority; in dpci_get_rx_queue()
408 uint8_t priority, in dpci_get_tx_queue() argument
421 cmd_params->priority = priority; in dpci_get_tx_queue()
H A Dfsl_dpdmai.h145 uint8_t priority; member
182 uint8_t priority,
203 uint8_t priority,
220 uint8_t priority,
H A Dfsl_dpci.h144 uint8_t priority; member
188 uint8_t priority,
207 uint8_t priority,
224 uint8_t priority,
/dpdk/drivers/net/i40e/base/
H A Di40e_dcb.c43 u8 priority; in i40e_parse_ieee_etscfg_tlv() local
113 u8 priority; in i40e_parse_ieee_etsrec_tlv() local
285 u8 priority; in i40e_parse_cee_pgcfg_tlv() local
387 dcbcfg->app[i].priority = up; in i40e_parse_cee_app_tlv()
647 dcbcfg->app[0].priority = in i40e_cee_to_dcb_v1_config()
654 dcbcfg->app[1].priority = in i40e_cee_to_dcb_v1_config()
661 dcbcfg->app[2].priority = in i40e_cee_to_dcb_v1_config()
728 dcbcfg->app[i].priority = in i40e_cee_to_dcb_config()
744 dcbcfg->app[i].priority = in i40e_cee_to_dcb_config()
760 dcbcfg->app[i].priority = in i40e_cee_to_dcb_config()
[all …]
/dpdk/examples/ip_pipeline/examples/
H A Dfirewall.cli56 pipeline PIPELINE0 table 0 rule add match acl priority 0 ipv4 0.0.0.0 0 100.0.0.0 10 0 65535 0 6553…
57 pipeline PIPELINE0 table 0 rule add match acl priority 0 ipv4 0.0.0.0 0 100.64.0.0 10 0 65535 0 655…
58 pipeline PIPELINE0 table 0 rule add match acl priority 0 ipv4 0.0.0.0 0 100.128.0.0 10 0 65535 0 65…
59 pipeline PIPELINE0 table 0 rule add match acl priority 0 ipv4 0.0.0.0 0 100.192.0.0 10 0 65535 0 65…
/dpdk/drivers/event/cnxk/
H A Dcnxk_eventdev.c296 queue_conf->priority = RTE_EVENT_DEV_PRIORITY_NORMAL; in cnxk_sso_queue_def_conf()
304 uint8_t priority, weight, affinity; in cnxk_sso_queue_setup() local
310 priority = CNXK_QOS_NORMALIZE(queue_conf->priority, 0, in cnxk_sso_queue_setup()
321 priority, weight, affinity); in cnxk_sso_queue_setup()
324 priority); in cnxk_sso_queue_setup()
355 uint8_t priority, weight, affinity; in cnxk_sso_queue_attribute_set() local
362 conf->priority = attr_value; in cnxk_sso_queue_attribute_set()
382 priority = CNXK_QOS_NORMALIZE(conf->priority, 0, in cnxk_sso_queue_attribute_set()
393 priority); in cnxk_sso_queue_attribute_set()
/dpdk/drivers/common/cnxk/
H A Droc_nix_mcast.c19 uint8_t priority, uint16_t index[]) in roc_nix_mcast_mcam_entry_alloc() argument
29 req->priority = priority; in roc_nix_mcast_mcam_entry_alloc()
H A Droc_nix_tm.c201 priority = node->priority; in nix_tm_node_add()
1331 node->priority = 0; in nix_tm_prepare_default_tree()
1358 node->priority = 0; in nix_tm_prepare_default_tree()
1399 node->priority = 0; in roc_nix_tm_prepare_rate_limited_tree()
1425 node->priority = 0; in roc_nix_tm_prepare_rate_limited_tree()
1450 node->priority = 0; in roc_nix_tm_prepare_rate_limited_tree()
1490 node->priority = 0; in roc_nix_tm_pfc_prepare_tree()
1512 node->priority = 0; in roc_nix_tm_pfc_prepare_tree()
1536 node->priority = 0; in roc_nix_tm_pfc_prepare_tree()
1561 node->priority = 0; in roc_nix_tm_pfc_prepare_tree()
[all …]
H A Droc_nix_tm_utils.c95 if (child_node->priority == child_node->parent->rr_prio) in nix_tm_find_prio_anchor()
97 return child_node->hw_id - child_node->priority; in nix_tm_find_prio_anchor()
358 uint32_t priority; in nix_tm_check_rr() local
372 priority = node->priority; in nix_tm_check_rr()
373 node_cnt[priority]++; in nix_tm_check_rr()
421 uint32_t priority, enum roc_nix_tm_tree tree) in nix_tm_validate_prio() argument
431 if (priority > nix_tm_max_prio(nix, nix_tm_lvl2nix(nix, lvl - 1))) in nix_tm_validate_prio()
438 priorities[priority] = 1; in nix_tm_validate_prio()
447 priorities[node->priority]++; in nix_tm_validate_prio()
459 if (priority && !priorities[priority - 1]) in nix_tm_validate_prio()
[all …]
/dpdk/drivers/net/dpaa2/
H A Ddpaa2_tm.c360 __rte_unused uint32_t priority, uint32_t weight, in dpaa2_node_check_params() argument
433 uint32_t parent_node_id, uint32_t priority, uint32_t weight, in dpaa2_node_add() argument
447 ret = dpaa2_node_check_params(dev, node_id, priority, weight, level_id, in dpaa2_node_add()
519 node->priority = priority; in dpaa2_node_add()
657 nodes[n - 1]->id, nodes[n - 1]->priority, in dpaa2_tm_sort_and_configure()
664 if (nodes[i]->priority > nodes[i + 1]->priority) { in dpaa2_tm_sort_and_configure()
673 nodes[n - 1]->id, nodes[n - 1]->priority, in dpaa2_tm_sort_and_configure()
807 if (leaf_node->priority == temp_leaf_node->priority) { in dpaa2_hierarchy_commit()
841 prio_cfg.prio_group_A = leaf_node->priority; in dpaa2_hierarchy_commit()
847 prio_cfg.prio_group_B = leaf_node->priority; in dpaa2_hierarchy_commit()
/dpdk/doc/guides/sample_app_ug/
H A Dl3_forward_access_ctrl.rst80 * priority field: A weight to measure the priority of the rules.
82 Rules with lower priority will NEVER be returned in any cases.
112 * Rules are organized in descending order of priority,
113 …which means rules at the head of the file always have a higher priority than those further down in…
162 As described earlier, the application assume rules are listed in descending order of priority,
163 therefore Rule 1 has the highest priority, then Rule 2, and finally,
164 Rule 3 has the lowest priority.
182 For priority reasons, Packet 1 matches Rule 1 and is dropped.
315 The application needs to consider the userdata and priority fields.
319 As for the priority field, the application assumes rules are organized in descending order of prior…
[all …]
H A Dvmdq_dcb_forwarding.rst18 address, VLAN ID and VLAN user priority fields.
20 …B places each packet into one of queues within that group, based upon the VLAN user priority field.
105 and dividing up the possible user priority values equally among the individual queues
107 if the number of pools is 32, then the user priority fields are allocated 2 to a queue.
108 If 16 pools are used, then each of the 8 user priority fields is allocated to its own queue within …
110 then the user priority fields are allocated 2 to one tc, and a tc has 2 queues mapping to it, then
120 :start-after: Dividing up the possible user priority values. 8<
121 :end-before: >8 End of dividing up the possible user priority values.
/dpdk/drivers/net/igc/
H A Digc_flow.c94 if (attr->priority == 0) in igc_parse_attribute()
101 if (IGC_IS_ALL_BITS_SET(attr->priority)) { in igc_parse_attribute()
108 if (attr->priority > IGC_NTUPLE_MAX_PRI) in igc_parse_attribute()
113 if (attr->priority > 1) { in igc_parse_attribute()
118 filter->ntuple.tuple_info.priority = (uint8_t)attr->priority; in igc_parse_attribute()
123 filter->ntuple.tuple_info.priority = (uint8_t)attr->priority; in igc_parse_attribute()
124 filter->syn.hig_pri = (uint8_t)attr->priority; in igc_parse_attribute()
/dpdk/drivers/net/softnic/
H A Drte_eth_softnic_tm.c1428 uint32_t priority, in node_add_check_port() argument
1447 if (priority != 0) in node_add_check_port()
1502 uint32_t priority, in node_add_check_subport() argument
1519 if (priority != 0) in node_add_check_subport()
1574 uint32_t priority, in node_add_check_pipe() argument
1591 if (priority != 0) in node_add_check_pipe()
1724 uint32_t priority, in node_add_check_queue() argument
1741 if (priority != 0) in node_add_check_queue()
1994 n->priority = priority; in pmd_tm_node_add()
2645 nt->priority != nt_any->priority || in hierarchy_commit_check()
[all …]
/dpdk/doc/guides/dmadevs/
H A Didxd.rst53 such as priority or queue depth, need to be set for each queue.
64 * priority: WQ priority between 1 and 15. Larger value means higher priority.
72 --mode=dedicated --priority=10 --wq-size=8 \
97 --priority=10 --max-batch-size=1024 --mode=dedicated --name=dpdk_app1
99 --priority=10 --max-batch-size=1024 --mode=dedicated --name=dpdk_app1
101 --priority=10 --max-batch-size=1024 --mode=dedicated --name=dpdk_app1
103 --priority=10 --max-batch-size=1024 --mode=dedicated --name=dpdk_app1
/dpdk/examples/flow_classify/
H A Dflow_classify.c472 ntuple_filter->priority = (uint16_t)temp; in parse_ipv4_5tuple_rule()
473 if (ntuple_filter->priority > FLOW_CLASSIFY_MAX_PRIORITY) in parse_ipv4_5tuple_rule()
578 attr.priority = ntuple_filter->priority; in add_classify_rule()
601 attr.priority = ntuple_filter->priority; in add_classify_rule()
626 attr.priority = ntuple_filter->priority; in add_classify_rule()
/dpdk/drivers/net/ipn3ke/
H A Dipn3ke_tm.c140 nodes->priority = IPN3KE_TM_NODE_PRIORITY_NORMAL0; in ipn3ke_hw_tm_init()
157 nodes->priority = IPN3KE_TM_NODE_PRIORITY_NORMAL0; in ipn3ke_hw_tm_init()
1028 if (priority > IPN3KE_TM_NODE_PRIORITY_HIGHEST) in ipn3ke_tm_node_add_check_parameter()
1194 priority, in ipn3ke_tm_node_add()
1303 n->priority = priority; in ipn3ke_tm_node_add()
1617 n->priority, in ipn3ke_hw_tm_node_wr()
1648 n->priority, in ipn3ke_hw_tm_node_wr()
1700 n->priority, in ipn3ke_hw_tm_node_wr()
1881 n->priority = IPN3KE_TM_NODE_PRIORITY_NORMAL0; in ipn3ke_tm_hierarchy_commit_clear()
1895 n->priority = IPN3KE_TM_NODE_PRIORITY_NORMAL0; in ipn3ke_tm_hierarchy_commit_clear()
[all …]

12345678910>>...13