Home
last modified time | relevance | path

Searched refs:lsb (Results 1 – 11 of 11) sorted by relevance

/dpdk/lib/fib/
H A Dtrie_avx512.c75 const __m512i lsb = _mm512_set1_epi32(1); in trie_vec_lookup_x16x2() local
131 msk_ext_1 = _mm512_test_epi32_mask(res_1, lsb); in trie_vec_lookup_x16x2()
132 msk_ext_2 = _mm512_test_epi32_mask(res_2, lsb); in trie_vec_lookup_x16x2()
177 new_msk_1 = _mm512_test_epi32_mask(tmp_1, lsb); in trie_vec_lookup_x16x2()
178 new_msk_2 = _mm512_test_epi32_mask(tmp_2, lsb); in trie_vec_lookup_x16x2()
188 shuf_idxes = _mm512_maskz_add_epi8(k, shuf_idxes, lsb); in trie_vec_lookup_x16x2()
221 const __m512i lsb = _mm512_set1_epi32(1); in trie_vec_lookup_x8x2_8b() local
258 msk_ext_1 = _mm512_test_epi64_mask(res_1, lsb); in trie_vec_lookup_x8x2_8b()
259 msk_ext_2 = _mm512_test_epi64_mask(res_2, lsb); in trie_vec_lookup_x8x2_8b()
285 new_msk_1 = _mm512_test_epi64_mask(tmp_1, lsb); in trie_vec_lookup_x8x2_8b()
[all …]
H A Ddir24_8_avx512.c20 const __m512i lsb = _mm512_set1_epi32(1); in dir24_8_vec_lookup_x16() local
48 msk_ext = _mm512_test_epi32_mask(res, lsb); in dir24_8_vec_lookup_x16()
86 const __m512i lsb = _mm512_set1_epi64(1); in dir24_8_vec_lookup_x8_8b() local
99 msk_ext = _mm512_test_epi64_mask(res, lsb); in dir24_8_vec_lookup_x8_8b()
/dpdk/drivers/net/i40e/base/
H A Di40e_lan_hmc.c673 u16 lsb; member
747 shift_width = ce_info->lsb % 8; in i40e_write_byte()
788 shift_width = ce_info->lsb % 8; in i40e_write_word()
832 shift_width = ce_info->lsb % 8; in i40e_write_dword()
884 shift_width = ce_info->lsb % 8; in i40e_write_qword()
932 shift_width = ce_info->lsb % 8; in i40e_read_byte()
939 src = hmc_bits + (ce_info->lsb / 8); in i40e_read_byte()
970 shift_width = ce_info->lsb % 8; in i40e_read_word()
977 src = hmc_bits + (ce_info->lsb / 8); in i40e_read_word()
1014 shift_width = ce_info->lsb % 8; in i40e_read_dword()
[all …]
/dpdk/drivers/net/nfp/nfpcore/nfp-common/
H A Dnfp_cppat.h30 _nic_mask64(int msb, int lsb, int at0) in _nic_mask64() argument
33 int w = msb - lsb + 1; in _nic_mask64()
38 if ((lsb + w) > 64) in _nic_mask64()
46 return v << lsb; in _nic_mask64()
/dpdk/drivers/crypto/ccp/
H A Dccp_dev.c286 if (cmd_q->lsb >= 0) { in ccp_lsb_alloc()
292 return start + cmd_q->lsb * LSB_SIZE; in ccp_lsb_alloc()
326 if (cmd_q->lsb == lsbno) { in ccp_lsb_free()
408 cmd_q->lsb = bitno; in ccp_find_and_assign_lsb_to_q()
584 cmd_q->lsb = -1; in ccp_add_device()
H A Dccp_dev.h209 int lsb; member
/dpdk/drivers/net/ice/base/
H A Dice_common.c4399 shift_width = ce_info->lsb % 8; in ice_write_byte()
4439 shift_width = ce_info->lsb % 8; in ice_write_word()
4482 shift_width = ce_info->lsb % 8; in ice_write_dword()
4533 shift_width = ce_info->lsb % 8; in ice_write_qword()
4674 shift_width = ce_info->lsb % 8; in ice_read_byte()
4681 src = src_ctx + (ce_info->lsb / 8); in ice_read_byte()
4711 shift_width = ce_info->lsb % 8; in ice_read_word()
4718 src = src_ctx + (ce_info->lsb / 8); in ice_read_word()
4754 shift_width = ce_info->lsb % 8; in ice_read_dword()
4769 src = src_ctx + (ce_info->lsb / 8); in ice_read_dword()
[all …]
H A Dice_lan_tx_rx.h974 u16 lsb; member
981 .lsb = _lsb, \
/dpdk/drivers/net/ngbe/base/
H A Dngbe_regs.h1399 u64 lsb = rd32(hw, reg); in rd64() local
1401 return (lsb | msb << 32); in rd64()
/dpdk/drivers/net/txgbe/base/
H A Dtxgbe_regs.h1841 u64 lsb = rd32(hw, reg); in rd64() local
1843 return (lsb | msb << 32); in rd64()
/dpdk/drivers/net/ixgbe/
H A Dixgbe_ethdev.c362 #define UPDATE_VF_STAT_36BIT(lsb, msb, last, cur) \ argument
364 u64 new_lsb = IXGBE_READ_REG(hw, lsb); \