Home
last modified time | relevance | path

Searched refs:pdata (Results 1 – 25 of 27) sorted by relevance

12

/dpdk/drivers/net/axgbe/
H A Daxgbe_mdio.c97 pdata->hw_if.set_speed(pdata, SPEED_2500); in axgbe_kx_2500_mode()
106 pdata->hw_if.set_speed(pdata, SPEED_1000); in axgbe_kx_1000_mode()
200 axgbe_change_mode(pdata, pdata->phy_if.phy_impl.switch_mode(pdata)); in axgbe_switch_mode()
290 pdata->phy_if.phy_impl.an_pre(pdata); in axgbe_an_restart()
577 pdata->an_result = pdata->an_state; in axgbe_an73_state_machine()
636 pdata->an_result = pdata->an_state; in axgbe_an37_state_machine()
807 pdata->an_mode = pdata->phy_if.phy_impl.an_mode(pdata); in axgbe_an_init()
859 mode = pdata->phy_if.phy_impl.get_mode(pdata, pdata->phy.speed); in axgbe_phy_config_fixed()
1050 pdata->phy.link = pdata->phy_if.phy_impl.link_status(pdata, in axgbe_phy_status()
1113 pdata->phy_if.phy_impl.stop(pdata); in axgbe_phy_stop()
[all …]
H A Daxgbe_dev.c172 XPCS32_IOWRITE(pdata, pdata->xpcs_window_sel_reg, index); in axgbe_read_mmd_regs_v2()
206 XPCS32_IOWRITE(pdata, pdata->xpcs_window_sel_reg, index); in axgbe_write_mmd_regs_v2()
826 AXGMAC_IOWRITE(pdata, MAC_RSSCR, pdata->rss_options); in axgbe_enable_rss()
1115 qptc = pdata->tx_q_count / pdata->hw_feat.tc_cnt; in axgbe_config_queue_mapping()
1116 qptc_extra = pdata->tx_q_count % pdata->hw_feat.tc_cnt; in axgbe_config_queue_mapping()
1260 axgbe_set_mac_address(pdata, pdata->mac_addr.addr_bytes); in axgbe_config_mac_address()
1274 axgbe_set_speed(pdata, pdata->phy_speed); in axgbe_config_mac_speed()
1326 axgbe_config_tsf_mode(pdata, pdata->tx_sf_mode); in axgbe_init()
1327 axgbe_config_rsf_mode(pdata, pdata->rx_sf_mode); in axgbe_init()
1328 axgbe_config_tx_threshold(pdata, pdata->tx_threshold); in axgbe_init()
[all …]
H A Daxgbe_ethdev.c281 return pdata->phy_if.phy_reset(pdata); in axgbe_phy_reset()
303 pdata->phy_if.an_isr(pdata); in axgbe_dev_interrupt_handler()
374 ret = pdata->hw_if.init(pdata); in axgbe_dev_start()
384 pdata->phy_if.phy_start(pdata); in axgbe_dev_start()
422 pdata->phy_if.phy_stop(pdata); in axgbe_dev_stop()
423 pdata->hw_if.exit(pdata); in axgbe_dev_stop()
765 pdata->phy_if.phy_status(pdata); in axgbe_dev_link_update()
1326 pdata->phy.tx_pause = pdata->tx_pause; in axgbe_flow_ctrl_set()
1327 pdata->phy.rx_pause = pdata->rx_pause; in axgbe_flow_ctrl_set()
2302 ret = pdata->hw_if.exit(pdata); in eth_axgbe_dev_init()
[all …]
H A Daxgbe_phy_impl.c263 return pdata->i2c_if.i2c_xfer(pdata, i2c_op); in axgbe_phy_i2c_xfer()
466 pdata->phy.advertising = pdata->phy.supported; in axgbe_phy_sfp_phy_settings()
1158 return pdata->hw_if.write_ext_mii_regs(pdata, phy_data->redrv_addr, in axgbe_phy_set_redrv_mode_mdio()
1551 cur_mode = axgbe_phy_get_mode(pdata, pdata->phy.speed); in axgbe_phy_check_mode()
1940 axgbe_phy_rrc(pdata); in axgbe_phy_cdr_notrack()
2016 pdata->i2c_if.i2c_stop(pdata); in axgbe_phy_stop()
2025 ret = pdata->i2c_if.i2c_start(pdata); in axgbe_phy_start()
2043 pdata->phy.advertising &= axgbe_phy_an_advertising(pdata); in axgbe_phy_start()
2074 ret = pdata->i2c_if.i2c_init(pdata); in axgbe_phy_init()
2277 ret = pdata->hw_if.set_ext_mii_mode(pdata, phy_data->mdio_addr, in axgbe_phy_init()
[all …]
H A Daxgbe_i2c.c106 tx_slots = pdata->i2c.tx_fifo_size - XI2C_IOREAD(pdata, IC_TXFLR); in axgbe_i2c_write()
181 axgbe_i2c_read(pdata); in axgbe_i2c_isr()
184 axgbe_i2c_write(pdata); in axgbe_i2c_isr()
266 if (axgbe_i2c_isr(pdata)) in axgbe_i2c_xfer()
273 axgbe_i2c_disable(pdata); in axgbe_i2c_xfer()
293 if (!pdata->i2c.started) in axgbe_i2c_stop()
298 pdata->i2c.started = 0; in axgbe_i2c_stop()
300 axgbe_i2c_disable(pdata); in axgbe_i2c_stop()
306 if (pdata->i2c.started) in axgbe_i2c_start()
311 pdata->i2c.started = 1; in axgbe_i2c_start()
[all …]
H A Daxgbe_regs.h157 for (i = 0; i < pdata->tx_ring_count; i++) in axgbe_regs_get_count()
159 for (i = 0; i < pdata->rx_ring_count; i++) in axgbe_regs_get_count()
162 for (i = 0; i < pdata->tx_q_count; i++) in axgbe_regs_get_count()
164 for (i = 0; i < pdata->rx_q_count; i++) in axgbe_regs_get_count()
182 for (j = 0; j < pdata->tx_ring_count; j++) { in axgbe_regs_dump()
186 *data++ = AXGMAC_IOREAD(pdata, reg); in axgbe_regs_dump()
194 *data++ = AXGMAC_IOREAD(pdata, reg); in axgbe_regs_dump()
201 for (j = 0; j < pdata->tx_q_count; j++) { in axgbe_regs_dump()
205 *data++ = AXGMAC_IOREAD(pdata, reg); in axgbe_regs_dump()
209 for (j = 0; j < pdata->rx_q_count; j++) { in axgbe_regs_dump()
[all …]
H A Daxgbe_rxtx.c55 rx_desc > pdata->rx_desc_count) in axgbe_dev_rx_queue_setup()
68 rxq->pdata = pdata; in axgbe_dev_rx_queue_setup()
112 if (!pdata->rx_queues) in axgbe_dev_rx_queue_setup()
161 axgbe_prepare_rx_stop(pdata, i); in axgbe_dev_disable_rx()
193 if (pdata->crc_strip_enable) { in axgbe_dev_enable_rx()
528 struct axgbe_port *pdata; in axgbe_dev_tx_queue_setup() local
535 pdata = dev->data->dev_private; in axgbe_dev_tx_queue_setup()
551 txq->pdata = pdata; in axgbe_dev_tx_queue_setup()
597 if (!pdata->tx_queues) in axgbe_dev_tx_queue_setup()
616 struct axgbe_port *pdata; in axgbe_dev_fw_version_get() local
[all …]
H A Daxgbe_ethdev.h689 void axgbe_set_mac_addn_addr(struct axgbe_port *pdata, u8 *addr,
691 void axgbe_set_mac_hash_table(struct axgbe_port *pdata, u8 *addr, bool add);
692 int axgbe_write_rss_lookup_table(struct axgbe_port *pdata);
693 int axgbe_write_rss_hash_key(struct axgbe_port *pdata);
H A Daxgbe_rxtx.h69 struct axgbe_port *pdata; member
109 struct axgbe_port *pdata; member
/dpdk/lib/acl/
H A Dacl_run_avx512_common.h164 p[0] = _M_I_(add_epi64)(p[0], pdata[0]); in _F_()
165 p[1] = _M_I_(add_epi64)(p[1], pdata[1]); in _F_()
185 _T_simd pdata[2], _T_simd *idx, _T_simd *di) in _F_()
210 pdata[0] = _M_I_(mask_expand_epi64)(pdata[0], m[0], nd[0]); in _F_()
211 pdata[1] = _M_I_(mask_expand_epi64)(pdata[1], m[1], nd[1]); in _F_()
316 pdata[0] = _M_SI_(setzero)(); in _F_()
317 pdata[1] = _M_SI_(setzero)(); in _F_()
318 pdata[2] = _M_SI_(setzero)(); in _F_()
319 pdata[3] = _M_SI_(setzero)(); in _F_()
342 &pdata[0], &idx[0], &di[0]); in _F_()
[all …]
H A Dacl_run_avx512x8.h157 _m256_mask_gather_epi8x4(__m256i pdata, __mmask8 mask) in _m256_mask_gather_epi8x4() argument
164 p.y = _mm256_mask_set1_epi64(pdata, mask ^ _SIMD_PTR_MSK_, in _m256_mask_gather_epi8x4()
H A Dacl_run_avx512x16.h193 _m512_mask_gather_epi8x8(__m512i pdata, __mmask8 mask) in _m512_mask_gather_epi8x8() argument
200 p.z = _mm512_mask_set1_epi64(pdata, mask ^ _SIMD_PTR_MSK_, in _m512_mask_gather_epi8x8()
/dpdk/app/test/
H A Dtest_distributor_perf.c69 volatile uint64_t *pdata = &data[0]; in time_cache_line_switch() local
70 *pdata = 1; in time_cache_line_switch()
72 while (*pdata) in time_cache_line_switch()
77 while (*pdata) in time_cache_line_switch()
79 *pdata = 1; in time_cache_line_switch()
83 while (*pdata) in time_cache_line_switch()
85 *pdata = 2; in time_cache_line_switch()
H A Dtest_rcu_qsbr_perf.c292 uint32_t *pdata; in test_rcu_qsbr_hash_reader() local
306 (void **)&pdata) != -ENOENT) { in test_rcu_qsbr_hash_reader()
307 pdata[thread_id] = 0; in test_rcu_qsbr_hash_reader()
308 while (pdata[thread_id] < COUNTER_VALUE) in test_rcu_qsbr_hash_reader()
309 pdata[thread_id]++; in test_rcu_qsbr_hash_reader()
H A Dtest_rcu_qsbr.c970 uint32_t *pdata; in test_rcu_qsbr_reader() local
982 (void **)&pdata) != -ENOENT) { in test_rcu_qsbr_reader()
983 pdata[lcore_id] = 0; in test_rcu_qsbr_reader()
984 while (pdata[lcore_id] < COUNTER_VALUE) in test_rcu_qsbr_reader()
985 pdata[lcore_id]++; in test_rcu_qsbr_reader()
/dpdk/drivers/net/sfc/
H A Dsfc_mae.c1257 et = &pdata->ethertypes[pdata->nb_vlan_tags]; in sfc_mae_set_ethertypes()
1274 et = &pdata->ethertypes[i]; in sfc_mae_set_ethertypes()
1425 pdata->has_ovlan_value); in sfc_mae_rule_process_pattern_data()
1434 pdata->has_ivlan_value); in sfc_mae_rule_process_pattern_data()
1992 &pdata->has_ovlan_mask, in sfc_mae_rule_parse_item_vlan()
1993 &pdata->has_ivlan_mask, in sfc_mae_rule_parse_item_vlan()
1996 &pdata->has_ovlan_value, in sfc_mae_rule_parse_item_vlan()
1997 &pdata->has_ivlan_value, in sfc_mae_rule_parse_item_vlan()
2061 pdata->tci_masks[pdata->nb_vlan_tags] = item_mask->tci; in sfc_mae_rule_parse_item_vlan()
2063 if (pdata->nb_vlan_tags == in sfc_mae_rule_parse_item_vlan()
[all …]
/dpdk/drivers/net/bnx2x/
H A Decore_init.h342 struct cmng_struct_per_port *pdata = &ram_data->port; in ecore_init_max() local
349 pdata->rs_vars.rs_periodic_timeout = in ecore_init_max()
356 pdata->rs_vars.rs_threshold = in ecore_init_max()
396 struct cmng_struct_per_port *pdata = &ram_data->port; in ecore_init_min() local
408 pdata->fair_vars.fair_threshold = QM_ARB_BYTES + in ecore_init_min()
412 pdata->fair_vars.size_thr = input_data->size_thr; in ecore_init_min()
421 pdata->fair_vars.fairness_timeout = in ecore_init_min()
443 pdata->fair_vars.fair_threshold + in ecore_init_min()
446 pdata->fair_vars.fair_threshold + in ecore_init_min()
482 if (ccd[cos] < pdata->fair_vars.fair_threshold in ecore_init_fw_wrr()
[all …]
H A Decore_init_ops.h81 uint64_t *pdata = ((uint64_t *)(GUNZIP_BUF(sc))) + i; in ecore_init_wr_64() local
83 *pdata = data64; in ecore_init_wr_64()
/dpdk/examples/qos_sched/
H A Dapp_thread.c35 uint16_t *pdata = rte_pktmbuf_mtod(m, uint16_t *); in get_pkt_sched() local
39 *subport = (rte_be_to_cpu_16(pdata[SUBPORT_OFFSET]) & 0x0FFF) & in get_pkt_sched()
43 *pipe = (rte_be_to_cpu_16(pdata[PIPE_OFFSET]) & 0x0FFF) & in get_pkt_sched()
46 pipe_queue = active_queues[(pdata[QUEUE_OFFSET] >> 8) % n_active_queues]; in get_pkt_sched()
56 *color = pdata[COLOR_OFFSET] & 0x03; in get_pkt_sched()
/dpdk/drivers/net/ipn3ke/
H A Dipn3ke_flow.c991 uint32_t *pdata = NULL; in ipn3ke_flow_hw_update() local
998 pdata = (uint32_t *)flow->rule.key; in ipn3ke_flow_hw_update()
1008 pdata = (uint32_t *)flow->rule.result; in ipn3ke_flow_hw_update()
1015 IPN3KE_AFU_PMD_DEBUG(" %02x", pdata[i]); in ipn3ke_flow_hw_update()
1018 pdata = (uint32_t *)flow->rule.key; in ipn3ke_flow_hw_update()
1023 ipn3ke_swap32(pdata[3]), in ipn3ke_flow_hw_update()
1029 ipn3ke_swap32(pdata[2]), in ipn3ke_flow_hw_update()
1035 ipn3ke_swap32(pdata[1]), in ipn3ke_flow_hw_update()
1041 ipn3ke_swap32(pdata[0]), in ipn3ke_flow_hw_update()
1044 pdata = (uint32_t *)flow->rule.result; in ipn3ke_flow_hw_update()
[all …]
/dpdk/drivers/net/ice/base/
H A Dice_switch.h72 (offsetof(struct ice_aqc_sw_rules_elem, pdata.lkup_tx_rx.hdr) + \
76 (offsetof(struct ice_aqc_sw_rules_elem, pdata.lkup_tx_rx.hdr))
78 (offsetof(struct ice_aqc_sw_rules_elem, pdata.lg_act.act) + \
81 (offsetof(struct ice_aqc_sw_rules_elem, pdata.vsi_list.vsi) + \
H A Dice_switch.c3720 s_rule->pdata.lkup_tx_rx.act = 0; in ice_fill_sw_rule()
3721 s_rule->pdata.lkup_tx_rx.index = in ice_fill_sw_rule()
3723 s_rule->pdata.lkup_tx_rx.hdr_len = 0; in ice_fill_sw_rule()
3919 rx_tx->pdata.lkup_tx_rx.act = in ice_add_marker_act()
3928 rx_tx->pdata.lkup_tx_rx.index = in ice_add_marker_act()
4113 s_rule->pdata.vsi_list.vsi[i] = in ice_update_vsi_list_rule()
8489 pkt = s_rule->pdata.lkup_tx_rx.hdr; in ice_fill_adv_dummy_packet()
8961 s_rule->pdata.lkup_tx_rx.src = in ice_add_adv_rule()
8979 s_rule->pdata.lkup_tx_rx.hdr, in ice_add_adv_rule()
9207 s_rule->pdata.lkup_tx_rx.act = 0; in ice_rem_adv_rule()
[all …]
/dpdk/drivers/net/pfe/
H A Dpfe_ethdev.c834 struct ls1012a_pfe_platform_data *pdata) in pfe_get_gemac_if_proprties() argument
856 pdata->ls1012a_eth_pdata[port].gem_id = port; in pfe_get_gemac_if_proprties()
861 memcpy(pdata->ls1012a_eth_pdata[port].mac_addr, mac_addr, in pfe_get_gemac_if_proprties()
870 pdata->ls1012a_eth_pdata[port].mdio_muxval = phy_id; in pfe_get_gemac_if_proprties()
872 if (pdata->ls1012a_eth_pdata[port].phy_id < 32) in pfe_get_gemac_if_proprties()
873 pfe->mdio_muxval[pdata->ls1012a_eth_pdata[port].phy_id] = in pfe_get_gemac_if_proprties()
874 pdata->ls1012a_eth_pdata[port].mdio_muxval; in pfe_get_gemac_if_proprties()
/dpdk/lib/hash/
H A Drte_cuckoo_hash.c709 __atomic_store_n(&k->pdata, in search_and_update()
1072 __atomic_store_n(&new_k->pdata, in __rte_hash_add_key_with_hash()
1256 *data = k->pdata; in search_one_bucket_l()
1295 &k->pdata, in search_one_bucket_lf()
1489 key_data = k->pdata; in __hash_rcu_qsbr_free_resource()
1971 data[i] = key_slot->pdata; in __bulk_lookup_l()
2000 data[i] = key_slot->pdata; in __bulk_lookup_l()
2130 &key_slot->pdata, in __bulk_lookup_lf()
2163 &key_slot->pdata, in __bulk_lookup_lf()
2505 *data = next_key->pdata; in rte_hash_iterate()
[all …]
H A Drte_cuckoo_hash.h140 void *pdata; member

12