| /dpdk/app/test/ |
| H A D | test_acl.h | 84 .priority = 1},
90 .priority = 1},
97 .priority = 1},
103 .priority = 1},
110 .priority = 1},
116 .priority = 1},
144 .priority = 230},
155 .priority = 330},
166 .priority = 230},
179 .priority = 240},
[all …]
|
| H A D | test_threads.c | 83 enum rte_thread_priority priority; in test_thread_priority() local
92 priority = RTE_THREAD_PRIORITY_NORMAL; in test_thread_priority()
93 RTE_TEST_ASSERT(rte_thread_set_priority(thread_id, priority) == 0, in test_thread_priority()
95 RTE_TEST_ASSERT(rte_thread_get_priority(thread_id, &priority) == 0, in test_thread_priority()
97 RTE_TEST_ASSERT(priority == RTE_THREAD_PRIORITY_NORMAL, in test_thread_priority()
100 priority = RTE_THREAD_PRIORITY_REALTIME_CRITICAL; in test_thread_priority()
102 RTE_TEST_ASSERT(rte_thread_set_priority(thread_id, priority) == ENOTSUP, in test_thread_priority()
104 RTE_TEST_ASSERT(rte_thread_get_priority(thread_id, &priority) == 0, in test_thread_priority()
106 RTE_TEST_ASSERT(priority == RTE_THREAD_PRIORITY_NORMAL, in test_thread_priority()
109 RTE_TEST_ASSERT(rte_thread_set_priority(thread_id, priority) == 0, in test_thread_priority()
[all …]
|
| H A D | test_event_timer_adapter.c | 475 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_state()
533 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _arm_timers()
658 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _arm_timers_burst()
752 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_cancel_periodic()
794 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_cancel()
836 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _cancel_producer()
875 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in _cancel_producer_burst()
1054 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in test_timer_cancel_random()
1241 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in stat_inc_reset_ev_enq()
1316 .ev.priority = RTE_EVENT_DEV_PRIORITY_NORMAL, in event_timer_arm()
[all …]
|
| /dpdk/lib/acl/ |
| H A D | acl_run_scalar.c | 22 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()
40 if (saved_priority[i + 1] <= priority[i + 1]) { in resolve_priority_scalar()
41 saved_priority[i + 1] = priority[i + 1]; in resolve_priority_scalar()
44 if (saved_priority[i + 2] <= priority[i + 2]) { in resolve_priority_scalar()
45 saved_priority[i + 2] = priority[i + 2]; in resolve_priority_scalar()
48 if (saved_priority[i + 3] <= priority[i + 3]) { in resolve_priority_scalar()
[all …]
|
| H A D | acl_run_neon.h | 41 int32x4_t results, priority, results1, priority1; in resolve_priority_neon() local
47 saved_priority = (int32_t *)(&parms[n].cmplt->priority[x]); in resolve_priority_neon()
52 priority = vld1q_s32( in resolve_priority_neon()
53 (const int32_t *)&p[transition].priority[x]); in resolve_priority_neon()
62 selector = vcgtq_s32(priority1, priority); in resolve_priority_neon()
64 priority = vbslq_s32(selector, priority1, priority); in resolve_priority_neon()
69 vst1q_s32(saved_priority, priority); in resolve_priority_neon()
|
| H A D | acl_run.h | 60 int32_t priority[RTE_ACL_MAX_CATEGORIES]; /* running priorities. */ in __rte_aligned() local
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()
|
| H A D | acl_run_sse.h | 60 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 D | acl_run_altivec.h | 45 xmm_t results, priority, results1, priority1; in resolve_priority_altivec() local
53 (xmm_t *)(&parms[n].cmplt->priority[x]); in resolve_priority_altivec()
57 priority = *(const xmm_t *)&p[transition].priority[x]; in resolve_priority_altivec()
67 selector = vec_cmpgt(priority1, priority); in resolve_priority_altivec()
69 priority = vec_sel(priority, priority1, in resolve_priority_altivec()
75 *saved_priority = priority; in resolve_priority_altivec()
|
| /dpdk/drivers/bus/fslmc/mc/ |
| H A D | dpdmai.c | 327 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 D | dpci.c | 321 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 D | fsl_dpdmai.h | 145 uint8_t priority; member
182 uint8_t priority,
203 uint8_t priority,
220 uint8_t priority,
|
| H A D | fsl_dpci.h | 146 uint8_t priority; member
190 uint8_t priority,
209 uint8_t priority,
226 uint8_t priority,
|
| H A D | fsl_dpdmai_cmd.h | 85 uint8_t priority; member
95 uint8_t priority; member
|
| /dpdk/drivers/event/dlb2/ |
| H A D | dlb2_sse.c | 85 sched_word[0] = EV_TO_DLB2_PRIO(ev[0].priority) << 10 | in dlb2_event_build_hcws()
88 sched_word[1] = EV_TO_DLB2_PRIO(ev[1].priority) << 10 | in dlb2_event_build_hcws()
91 sched_word[2] = EV_TO_DLB2_PRIO(ev[2].priority) << 10 | in dlb2_event_build_hcws()
94 sched_word[3] = EV_TO_DLB2_PRIO(ev[3].priority) << 10 | in dlb2_event_build_hcws()
210 qe[i].priority = EV_TO_DLB2_PRIO(ev[i].priority); in dlb2_event_build_hcws()
218 info->priority = qe[i].priority; in dlb2_event_build_hcws()
|
| /dpdk/lib/eal/include/ |
| H A D | rte_thread.h | 69 enum rte_thread_priority priority; /**< thread priority */ member
275 enum rte_thread_priority priority);
383 enum rte_thread_priority *priority);
399 enum rte_thread_priority priority);
|
| H A D | rte_common.h | 315 * Run function before main() with high priority.
336 #define CTOR_PRIORITY_TO_SECTION(priority) CTOR_SECTION_ ## priority
338 #define RTE_INIT_PRIO(name, priority) \
341 __pragma(const_seg(CTOR_PRIORITY_TO_SECTION(priority))) \
342 __declspec(allocate(CTOR_PRIORITY_TO_SECTION(priority))) \
350 * Run function before main() with low priority.
361 * Run after main() with low priority.
379 #define DTOR_PRIORITY_TO_SECTION(priority) DTOR_SECTION_ ## priority
261 CTOR_PRIORITY_TO_SECTION(priority) global() argument
263 RTE_INIT_PRIO(name,priority) global() argument
304 DTOR_PRIORITY_TO_SECTION(priority) global() argument
306 RTE_FINI_PRIO(name,priority) global() argument
[all...] |
| /dpdk/lib/eal/unix/ |
| H A D | rte_thread.c | 47 * Choose the middle of the range to represent the priority in thread_map_priority_to_os_value()
60 EAL_LOG(DEBUG, "The requested priority value is invalid."); in thread_map_priority_to_os_value()
86 EAL_LOG(DEBUG, "The OS priority value does not map to an EAL-defined priority."); in thread_map_os_priority_to_eal_priority()
165 * otherwise the priority attribute is ignored. in rte_thread_create()
174 if (thread_attr->priority == in rte_thread_create()
179 ret = thread_map_priority_to_os_value(thread_attr->priority, in rte_thread_create()
277 enum rte_thread_priority *priority) in rte_thread_set_priority()
291 param.sched_priority, priority); in rte_thread_set_priority()
299 enum rte_thread_priority priority) in rte_thread_key_create()
252 rte_thread_get_priority(rte_thread_t thread_id,enum rte_thread_priority * priority) rte_thread_get_priority() argument
274 rte_thread_set_priority(rte_thread_t thread_id,enum rte_thread_priority priority) rte_thread_set_priority() argument
[all...] |
| /dpdk/examples/ip_pipeline/examples/ |
| H A D | firewall.cli | 56 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/net/mlx5/windows/ |
| H A D | mlx5_flow_os.h | 343 mlx5_flow_os_create_flow_action_send_to_kernel(void *tbl, uint16_t priority, in mlx5_flow_os_create_flow_action_send_to_kernel() argument
347 RTE_SET_USED(priority); in mlx5_flow_os_create_flow_action_send_to_kernel()
420 mlx5_os_flow_adjust_priority(struct rte_eth_dev *dev, int32_t priority, in mlx5_os_flow_adjust_priority() argument
424 RTE_SET_USED(priority); in mlx5_os_flow_adjust_priority()
|
| /dpdk/drivers/net/mlx5/linux/ |
| H A D | mlx5_flow_os.h | 385 mlx5_flow_os_create_flow_action_send_to_kernel(void *tbl, uint16_t priority, in mlx5_flow_os_create_flow_action_send_to_kernel() argument
389 priority); in mlx5_flow_os_create_flow_action_send_to_kernel()
496 mlx5_os_flow_adjust_priority(struct rte_eth_dev *dev, int32_t priority, in mlx5_os_flow_adjust_priority() argument
499 return mlx5_flow_adjust_priority(dev, priority, subpriority); in mlx5_os_flow_adjust_priority()
|
| /dpdk/drivers/net/bnxt/tf_core/ |
| H A D | tf_tcam.h | 59 uint32_t priority; member
119 uint32_t priority; member
|
| /dpdk/doc/guides/sample_app_ug/ |
| H A D | vmdq_dcb_forwarding.rst | 18 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/lib/ethdev/ |
| H A D | rte_mtr.c | 349 uint32_t priority, in rte_mtr_color_in_protocol_set() argument
355 mtr_id, proto, priority, error); in rte_mtr_color_in_protocol_set()
357 rte_mtr_trace_color_in_protocol_set(port_id, mtr_id, proto, priority, ret); in rte_mtr_color_in_protocol_set()
384 uint32_t *priority, in rte_mtr_color_in_protocol_priority_get() argument
390 mtr_id, proto, priority, error); in rte_mtr_color_in_protocol_priority_get()
|
| /dpdk/lib/eal/windows/ |
| H A D | rte_thread.c | 234 thread_attr->priority); in rte_thread_create()
369 enum rte_thread_priority *priority) in rte_thread_get_priority() argument
395 ret = thread_map_os_priority_to_eal_value(os_pri, pri_class, priority); in rte_thread_get_priority()
408 enum rte_thread_priority priority) in rte_thread_set_priority() argument
422 ret = thread_map_priority_to_os_value(priority, &os_priority, in rte_thread_set_priority()
|
| /dpdk/lib/eal/common/ |
| H A D | eal_common_thread.c | 415 attr->priority = RTE_THREAD_PRIORITY_NORMAL; in rte_thread_attr_init()
422 enum rte_thread_priority priority) in rte_thread_attr_set_priority() argument
427 thread_attr->priority = priority; in rte_thread_attr_set_priority()
|