| /f-stack/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}, 371 .priority = 1}, 678 .priority = 500 687 .priority = 400 696 .priority = 300 [all …]
|
| /f-stack/dpdk/lib/librte_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() 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 D | acl_run_neon.h | 39 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 D | acl_run_altivec.h | 43 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 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.h | 60 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()
|
| /f-stack/freebsd/contrib/openzfs/cmd/zed/ |
| H A D | zed_log.c | 32 int priority; member 162 zed_log_stderr_open(int priority) in zed_log_stderr_open() argument 165 _ctx.priority = priority; in zed_log_stderr_open() 205 _zed_log_aux(int priority, const char *fmt, va_list vargs) in _zed_log_aux() argument 220 syslog(priority, "%s", buf); in _zed_log_aux() 222 if (_ctx.do_stderr && (priority <= _ctx.priority)) in _zed_log_aux() 231 zed_log_msg(int priority, const char *fmt, ...) in zed_log_msg() argument 237 _zed_log_aux(priority, fmt, vargs); in zed_log_msg()
|
| H A D | zed_log.h | 32 void zed_log_stderr_open(int priority); 40 void zed_log_msg(int priority, const char *fmt, ...);
|
| /f-stack/freebsd/sys/ |
| H A D | taskqueue.h | 109 #define TASK_INITIALIZER(priority, func, context) \ argument 110 { .ta_priority = (priority), \ 123 #define TASK_INIT_FLAGS(task, priority, func, context, flags) do { \ argument 125 (task)->ta_priority = (priority); \ 134 struct timeout_task *timeout_task, int priority, task_fn_t func, 136 #define TIMEOUT_TASK_INIT(queue, timeout_task, priority, func, context) do { \ argument 137 _Static_assert((priority) >= 0 && (priority) <= 255, \ 139 _timeout_task_init(queue, timeout_task, priority, func, context); \
|
| H A D | gtaskqueue.h | 84 #define GTASK_INIT(gtask, flags, priority, func, context) do { \ argument 86 (gtask)->ta_priority = (priority); \ 91 #define GROUPTASK_INIT(gtask, priority, func, context) \ argument 92 GTASK_INIT(&(gtask)->gt_task, 0, priority, func, context)
|
| H A D | eventhandler.h | 122 #define EVENTHANDLER_DEFINE(name, func, arg, priority) \ argument 127 priority); \ 141 #define EVENTHANDLER_REGISTER(name, func, arg, priority) \ argument 142 eventhandler_register(NULL, #name, func, arg, priority) 161 const char *name, void *func, void *arg, int priority); 174 const char *name, void *func, void *arg, int priority,
|
| /f-stack/dpdk/drivers/bus/fslmc/mc/ |
| H A D | dpdmai.c | 325 uint8_t priority, in dpdmai_set_rx_queue() argument 337 cmd_params->dest_priority = cfg->dest_cfg.priority; in dpdmai_set_rx_queue() 338 cmd_params->priority = priority; in dpdmai_set_rx_queue() 367 uint8_t priority, in dpdmai_get_rx_queue() argument 380 cmd_params->priority = priority; in dpdmai_get_rx_queue() 393 attr->dest_cfg.priority = le32_to_cpu(rsp_params->dest_priority); in dpdmai_get_rx_queue() 417 uint8_t priority, in dpdmai_get_tx_queue() argument 430 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 | 126 uint8_t priority; member 163 uint8_t priority, 184 uint8_t priority, 201 uint8_t priority,
|
| H A D | fsl_dpci.h | 144 uint8_t priority; member 188 uint8_t priority, 207 uint8_t priority, 224 uint8_t priority,
|
| /f-stack/freebsd/contrib/ck/src/ |
| H A D | ck_ht.c | 453 if (priority != NULL) { in ck_ht_gc() 846 if (priority != NULL) { in ck_ht_set_spmc() 859 candidate = priority; in ck_ht_set_spmc() 864 priority != NULL && candidate != priority) { in ck_ht_set_spmc() 884 if (priority->value == CK_HT_KEY_TOMBSTONE) { in ck_ht_set_spmc() 913 if (priority != NULL) { in ck_ht_set_spmc() 914 if (priority->key == CK_HT_KEY_TOMBSTONE) { in ck_ht_set_spmc() 919 candidate = priority; in ck_ht_set_spmc() 982 if (candidate != NULL || priority != NULL) in ck_ht_put_spmc() 989 if (priority != NULL) { in ck_ht_put_spmc() [all …]
|
| /f-stack/freebsd/contrib/device-tree/Bindings/interrupt-controller/ |
| H A D | ti,c64x+megamod-pic.txt | 18 Single cell specifying the core interrupt priority level (4-15) where 19 4 is highest priority and 15 is lowest priority. 37 One for each core interrupt priority level. In addition to the combined 50 The cells contain the core priority interrupt to which the 56 priority interrupts. The first cell corresponds to 57 core priority 4 and the last cell corresponds to 58 core priority 15. The value of each cell is the 70 be the core priority level, not the megamodule interrupt number. 101 mapped directly to core priority interrupt 8. The node using this interrupt
|
| H A D | arm,nvic.txt | 5 vary in the number of interrupts and priority bits per interrupt. 19 The 2nd cell is the priority of the interrupt. 24 - arm,num-irq-priority-bits: The number of priority bits implemented by the 35 arm,num-irq-priority-bits = <4>;
|
| /f-stack/freebsd/kern/ |
| H A D | subr_devstat.c | 80 devstat_priority priority); 90 devstat_priority priority) in devstat_new_entry() argument 105 flags, device_type, priority); in devstat_new_entry() 120 devstat_priority priority) in devstat_add_entry() argument 153 if ((priority <= ds_tmp->priority) in devstat_add_entry() 155 || (priority > ds_next->priority))) { in devstat_add_entry() 159 } else if (priority > ds_tmp->priority) { in devstat_add_entry() 188 ds->priority = priority; in devstat_add_entry()
|
| /f-stack/dpdk/drivers/net/i40e/base/ |
| H A D | i40e_dcb.c | 43 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 381 dcbcfg->app[i].priority = up; in i40e_parse_cee_app_tlv() 641 dcbcfg->app[0].priority = in i40e_cee_to_dcb_v1_config() 648 dcbcfg->app[1].priority = in i40e_cee_to_dcb_v1_config() 655 dcbcfg->app[2].priority = in i40e_cee_to_dcb_v1_config() 722 dcbcfg->app[i].priority = in i40e_cee_to_dcb_config() 738 dcbcfg->app[i].priority = in i40e_cee_to_dcb_config() 754 dcbcfg->app[i].priority = in i40e_cee_to_dcb_config() [all …]
|
| /f-stack/freebsd/contrib/ncsw/Peripherals/FM/MAC/ |
| H A D | fman_memac.c | 281 uint8_t priority, in fman_memac_set_tx_pause_frames() argument 289 if (priority == 0xff) { in fman_memac_set_tx_pause_frames() 295 priority = 0; in fman_memac_set_tx_pause_frames() 306 tmp = ioread32be(®s->pause_quanta[priority / 2]); in fman_memac_set_tx_pause_frames() 307 if (priority % 2) in fman_memac_set_tx_pause_frames() 311 tmp |= ((uint32_t)pause_time << (16 * (priority % 2))); in fman_memac_set_tx_pause_frames() 312 iowrite32be(tmp, ®s->pause_quanta[priority / 2]); in fman_memac_set_tx_pause_frames() 314 tmp = ioread32be(®s->pause_thresh[priority / 2]); in fman_memac_set_tx_pause_frames() 315 if (priority % 2) in fman_memac_set_tx_pause_frames() 319 tmp |= ((uint32_t)thresh_time<<(16 * (priority % 2))); in fman_memac_set_tx_pause_frames() [all …]
|
| /f-stack/freebsd/contrib/device-tree/Bindings/thermal/ |
| H A D | nvidia,tegra124-soctherm.txt | 39 - nvidia,priority: Each throttles has its own throttle settings, so the 42 Bigger value indicates higher priority, In general, higher priority 44 thermal alarms are given higher priority, and ensure that there is 45 no race if priority of two vectors is set to the same value. 128 nvidia,priority = <100>; 141 nvidia,priority = <80>; 150 * arbiter will select the highest priority as the final throttle 155 nvidia,priority = <50>; 181 nvidia,priority = <100>; 192 nvidia,priority = <80>; [all …]
|
| /f-stack/freebsd/contrib/device-tree/Bindings/power/reset/ |
| H A D | gpio-restart.txt | 11 priority order. The gpio is configured as an output, and driven active, 31 - priority : A priority ranging from 0 to 255 (default 128) according to 38 255: Highest priority restart handler, will preempt all other 50 priority = <128>;
|
| /f-stack/freebsd/net/ |
| H A D | vnet.h | 378 #define VNET_GLOBAL_EVENTHANDLER_REGISTER_TAG(tag, name, func, arg, priority) \ argument 382 arg, priority, \ 386 #define VNET_GLOBAL_EVENTHANDLER_REGISTER(name, func, arg, priority) \ argument 390 arg, priority, \ 450 #define VNET_GLOBAL_EVENTHANDLER_REGISTER_TAG(tag, name, func, arg, priority) \ argument 451 (tag) = eventhandler_register(NULL, #name, func, arg, priority) 452 #define VNET_GLOBAL_EVENTHANDLER_REGISTER(name, func, arg, priority) \ argument 453 eventhandler_register(NULL, #name, func, arg, priority)
|
| /f-stack/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…
|