Home
last modified time | relevance | path

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

/dpdk/lib/net/
H A Dnet_crc_neon.c69 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
79 tmp2 = vshift_bytes_left(tmp0, 4); in crcr32_reduce_128_to_64()
81 vgetq_lane_p64(vreinterpretq_p64_u64(tmp2), 0), in crcr32_reduce_128_to_64()
105 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
115 tmp2 = vreinterpretq_u64_p128(vmull_p64( in crcr32_reduce_64_to_32()
118 tmp2 = veorq_u64(tmp2, tmp1); in crcr32_reduce_64_to_32()
119 tmp2 = veorq_u64(tmp2, tmp0); in crcr32_reduce_64_to_32()
121 return vgetq_lane_u32(vreinterpretq_u32_u64(tmp2), 2); in crcr32_reduce_64_to_32()
H A Dnet_crc_sse.c70 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
78 tmp2 = _mm_slli_si128(tmp0, 4); in crcr32_reduce_128_to_64()
79 tmp1 = _mm_clmulepi64_si128(tmp2, precomp, 0x10); in crcr32_reduce_128_to_64()
106 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
114 tmp2 = _mm_clmulepi64_si128(tmp1, precomp, 0x10); in crcr32_reduce_64_to_32()
115 tmp2 = _mm_xor_si128(tmp2, tmp1); in crcr32_reduce_64_to_32()
116 tmp2 = _mm_xor_si128(tmp2, tmp0); in crcr32_reduce_64_to_32()
118 return _mm_extract_epi32(tmp2, 2); in crcr32_reduce_64_to_32()
H A Dnet_crc_avx512.c65 __m512i tmp0, tmp1, tmp2, tmp3; in crc32_fold_128() local
74 tmp2 = _mm512_clmulepi64_epi128(fold1, params->fold_3x128b, 0x01); in crc32_fold_128()
77 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp1, tmp2, 0x96); in crc32_fold_128()
/dpdk/app/test/
H A Dtest_ipsec_sad.c431 uint64_t tmp1, tmp2, tmp3; in __test_lookup_adv() local
478 install_sa = &tmp2; in __test_lookup_adv()
485 RTE_TEST_ASSERT(sa[0] == &tmp2, in __test_lookup_adv()
487 RTE_TEST_ASSERT(sa[1] == &tmp2, in __test_lookup_adv()
522 install_sa = &tmp2; in __test_lookup_adv()
529 RTE_TEST_ASSERT(sa[0] == &tmp2, in __test_lookup_adv()
570 install_sa = &tmp2; in __test_lookup_adv()
603 install_sa = &tmp2; in __test_lookup_adv()
696 uint64_t tmp1, tmp2, tmp3; in __test_lookup_order() local
726 install_sa = &tmp2; in __test_lookup_order()
[all …]
H A Dtest_cmdline_cirbuf.c479 char tmp2[CMDLINE_TEST_BUFSIZE]; in test_cirbuf_string_get_del_partial() local
484 memset(tmp2, 0, sizeof(tmp)); in test_cirbuf_string_get_del_partial()
486 strlcpy(tmp2, CIRBUF_STR_HEAD, sizeof(tmp2)); in test_cirbuf_string_get_del_partial()
509 if (strncmp(tmp, tmp2, sizeof(CIRBUF_STR_HEAD) - 1) != 0) { in test_cirbuf_string_get_del_partial()
521 if (strncmp(tmp, &tmp2[1], sizeof(CIRBUF_STR_HEAD) - 1) != 0) { in test_cirbuf_string_get_del_partial()
545 if (strncmp(tmp, &tmp2[1], sizeof(CIRBUF_STR_HEAD) - 1) != 0) { in test_cirbuf_string_get_del_partial()
564 if (strncmp(tmp, &tmp2[1], sizeof(CIRBUF_STR_HEAD) - 2) != 0) { in test_cirbuf_string_get_del_partial()
/dpdk/lib/fib/
H A Dtrie_avx512.c15 __m512i tmp1, tmp2, tmp3, tmp4; in transpose_x16() local
25 tmp2 = _mm512_loadu_si512(&ips[4][0]); in transpose_x16()
30 tmp5 = _mm512_unpacklo_epi32(tmp1, tmp2); in transpose_x16()
31 tmp7 = _mm512_unpackhi_epi32(tmp1, tmp2); in transpose_x16()
37 tmp2 = _mm512_unpacklo_epi32(tmp7, tmp8); in transpose_x16()
45 *third = _mm512_permutexvar_epi32(perm_idxes.z, tmp2); in transpose_x16()
54 __m512i tmp1, tmp2, tmp3, tmp4; in transpose_x8() local
61 tmp2 = _mm512_loadu_si512(&ips[4][0]); in transpose_x8()
63 tmp3 = _mm512_unpacklo_epi64(tmp1, tmp2); in transpose_x8()
65 tmp4 = _mm512_unpackhi_epi64(tmp1, tmp2); in transpose_x8()
H A Ddir24_8_avx512.c22 __m512i tmp1, tmp2, res_msk; in dir24_8_vec_lookup_x16() local
73 tmp2 = _mm512_maskz_expand_epi32(exp_msk, in dir24_8_vec_lookup_x16()
76 _mm512_storeu_si512(next_hops + 8, tmp2); in dir24_8_vec_lookup_x16()
/dpdk/lib/bpf/
H A Dbpf_jit_arm64.c1020 emit_xadd(struct a64_jit_ctx *ctx, uint8_t op, uint8_t tmp1, uint8_t tmp2, in emit_xadd() argument
1037 emit_ldxr(ctx, is64, tmp2, rn); in emit_xadd()
1038 emit_add(ctx, is64, tmp2, src); in emit_xadd()
1039 emit_stxr(ctx, is64, tmp3, tmp2, rn); in emit_xadd()
1118 uint8_t op, dst, src, tmp1, tmp2, tmp3; in emit() local
1132 tmp2 = ebpf_to_a64_reg(ctx, TMP_REG_2); in emit()
1215 emit_mod(ctx, is64, tmp2, dst, tmp1); in emit()
1321 emit_mov_imm(ctx, 1, tmp2, off); in emit()
1322 emit_str(ctx, BPF_SIZE(op), tmp1, dst, tmp2); in emit()
1327 emit_xadd(ctx, op, tmp1, tmp2, tmp3, dst, off, src); in emit()
/dpdk/drivers/net/qede/base/
H A Decore_int.c240 u32 tmp, tmp2; in ecore_grc_attn_cb() local
255 tmp2 = ecore_rd(p_hwfn, p_hwfn->p_dpc_ptt, in ecore_grc_attn_cb()
260 tmp2, tmp, in ecore_grc_attn_cb()
267 (tmp2 & ECORE_GRC_ATTENTION_PF_MASK), in ecore_grc_attn_cb()
268 (((tmp2 & ECORE_GRC_ATTENTION_PRIV_MASK) >> in ecore_grc_attn_cb()
271 (tmp2 & ECORE_GRC_ATTENTION_VF_MASK) >> in ecore_grc_attn_cb()
/dpdk/drivers/net/ice/base/
H A Dice_flex_pipe.c2783 struct ice_vsig_prof *tmp2; in ice_match_prop_lst() local
2790 LIST_FOR_EACH_ENTRY(tmp2, list2, ice_vsig_prof, list) in ice_match_prop_lst()
2796 tmp2 = LIST_FIRST_ENTRY(list2, struct ice_vsig_prof, list); in ice_match_prop_lst()
2802 if (tmp2->profile_cookie != tmp1->profile_cookie) in ice_match_prop_lst()
2806 tmp2 = LIST_NEXT_ENTRY(tmp2, struct ice_vsig_prof, list); in ice_match_prop_lst()
/dpdk/drivers/net/bnx2x/
H A Delink.c10281 uint16_t tmp1, mod_abs, tmp2; in elink_8727_config_init() local
10346 MDIO_PMA_DEVAD, MDIO_PMA_REG_8727_OPT_CFG_REG, &tmp2); in elink_8727_config_init()
10347 tmp2 |= 0x1000; in elink_8727_config_init()
10348 tmp2 &= 0xFFEF; in elink_8727_config_init()
10350 MDIO_PMA_DEVAD, MDIO_PMA_REG_8727_OPT_CFG_REG, tmp2); in elink_8727_config_init()
10353 &tmp2); in elink_8727_config_init()
10356 (tmp2 & 0x7fff)); in elink_8727_config_init()