Home
last modified time | relevance | path

Searched refs:tmp1 (Results 1 – 12 of 12) sorted by relevance

/dpdk/lib/net/
H A Dnet_crc_neon.c69 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
75 tmp1 = vshift_bytes_right(data128, 8); in crcr32_reduce_128_to_64()
76 tmp0 = veorq_u64(tmp0, tmp1); in crcr32_reduce_128_to_64()
80 tmp1 = vreinterpretq_u64_p128(vmull_p64( in crcr32_reduce_128_to_64()
84 return veorq_u64(tmp1, tmp0); in crcr32_reduce_128_to_64()
105 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
109 tmp1 = vreinterpretq_u64_p128(vmull_p64( in crcr32_reduce_64_to_32()
112 tmp1 = veorq_u64(tmp1, tmp0); in crcr32_reduce_64_to_32()
113 tmp1 = vandq_u64(tmp1, vld1q_u64((uint64_t *)mask1)); in crcr32_reduce_64_to_32()
116 vgetq_lane_p64(vreinterpretq_p64_u64(tmp1), 0), in crcr32_reduce_64_to_32()
[all …]
H A Dnet_crc_sse.c70 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
74 tmp1 = _mm_srli_si128(data128, 8); in crcr32_reduce_128_to_64()
75 tmp0 = _mm_xor_si128(tmp0, tmp1); in crcr32_reduce_128_to_64()
79 tmp1 = _mm_clmulepi64_si128(tmp2, precomp, 0x10); in crcr32_reduce_128_to_64()
81 return _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_128_to_64()
106 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
110 tmp1 = _mm_clmulepi64_si128(tmp0, precomp, 0x00); in crcr32_reduce_64_to_32()
111 tmp1 = _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_64_to_32()
112 tmp1 = _mm_and_si128(tmp1, _mm_load_si128((const __m128i *)mask1)); in crcr32_reduce_64_to_32()
114 tmp2 = _mm_clmulepi64_si128(tmp1, precomp, 0x10); in crcr32_reduce_64_to_32()
[all …]
H A Dnet_crc_avx512.c51 __m512i tmp0, tmp1; in crcr32_folding_round() local
54 tmp1 = _mm512_clmulepi64_epi128(fold, precomp, 0x10); in crcr32_folding_round()
65 __m512i tmp0, tmp1, tmp2, tmp3; in crc32_fold_128() local
77 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp1, tmp2, 0x96); in crc32_fold_128()
80 tmp1 = _mm512_shuffle_i64x2(tmp0, tmp0, 0x4e); in crc32_fold_128()
143 __m128i tmp0, tmp1; in barrett_reduction() local
147 tmp1 = data64; in barrett_reduction()
153 tmp1 = data64; in barrett_reduction()
164 __m128i tmp, tmp1; in reduction_loop() local
169 tmp1 = _mm_loadu_si128((const __m128i *)&data[*n]); in reduction_loop()
[all …]
/dpdk/app/test/
H A Dtest_ipsec_sad.c431 uint64_t tmp1, tmp2, tmp3; in __test_lookup_adv() local
458 install_sa = &tmp1; in __test_lookup_adv()
465 RTE_TEST_ASSERT(sa[0] == &tmp1, in __test_lookup_adv()
467 RTE_TEST_ASSERT(sa[1] == &tmp1, in __test_lookup_adv()
469 RTE_TEST_ASSERT(sa[2] == &tmp1, in __test_lookup_adv()
518 install_sa = &tmp1; in __test_lookup_adv()
544 install_sa = &tmp1; in __test_lookup_adv()
599 install_sa = &tmp1; in __test_lookup_adv()
696 uint64_t tmp1, tmp2, tmp3; in __test_lookup_order() local
711 install_sa = &tmp1; in __test_lookup_order()
[all …]
H A Dtest_security.c906 void *tmp1[SECURITY_TEST_MEMPOOL_SIZE]; in test_session_create_mempool_empty() local
918 (void **)(&tmp1[i])); in test_session_create_mempool_empty()
941 (tmp1[i])); in test_session_create_mempool_empty()
/dpdk/lib/bpf/
H A Dbpf_jit_arm64.c1027 emit_mov_imm(ctx, 1, tmp1, off); in emit_xadd()
1028 emit_add(ctx, 1, tmp1, dst); in emit_xadd()
1029 rn = tmp1; in emit_xadd()
1169 emit_add(ctx, is64, dst, tmp1); in emit()
1180 emit_sub(ctx, is64, dst, tmp1); in emit()
1191 emit_mul(ctx, is64, dst, tmp1); in emit()
1203 emit_div(ctx, is64, dst, tmp1); in emit()
1226 emit_or(ctx, is64, dst, tmp1); in emit()
1237 emit_and(ctx, is64, dst, tmp1); in emit()
1345 emit_cmp(ctx, 1, dst, tmp1); in emit()
[all …]
/dpdk/lib/fib/
H A Dtrie_avx512.c15 __m512i tmp1, tmp2, tmp3, tmp4; in transpose_x16() local
24 tmp1 = _mm512_loadu_si512(&ips[0][0]); in transpose_x16()
30 tmp5 = _mm512_unpacklo_epi32(tmp1, tmp2); in transpose_x16()
31 tmp7 = _mm512_unpackhi_epi32(tmp1, tmp2); in transpose_x16()
35 tmp1 = _mm512_unpacklo_epi32(tmp5, tmp6); in transpose_x16()
41 *first = _mm512_permutexvar_epi32(perm_idxes.z, tmp1); in transpose_x16()
54 __m512i tmp1, tmp2, tmp3, tmp4; in transpose_x8() local
60 tmp1 = _mm512_loadu_si512(&ips[0][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
71 tmp1 = _mm512_maskz_expand_epi32(exp_msk, res); in dir24_8_vec_lookup_x16()
75 _mm512_storeu_si512(next_hops, tmp1); in dir24_8_vec_lookup_x16()
/dpdk/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_sse.c208 __m128i tmp0, tmp1, info3_v; in recv_burst_vec_sse() local
214 tmp1 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons + 2]); in recv_burst_vec_sse()
218 _mm_storeu_si128((void *)&rx_pkts[i + 2], tmp1); in recv_burst_vec_sse()
239 tmp1 = _mm_unpackhi_epi32(rxcmp1[2], rxcmp1[3]); in recv_burst_vec_sse()
252 info3_v = _mm_and_si128(_mm_unpacklo_epi64(tmp0, tmp1), in recv_burst_vec_sse()
/dpdk/lib/eal/arm/include/
H A Drte_pause_64.h102 [tmp1] "=&r" (dst_128->val[1]) \
108 [tmp1] "=&r" (dst_128->val[1]) \
/dpdk/drivers/net/ice/base/
H A Dice_flex_pipe.c2782 struct ice_vsig_prof *tmp1; in ice_match_prop_lst() local
2788 LIST_FOR_EACH_ENTRY(tmp1, list1, ice_vsig_prof, list) in ice_match_prop_lst()
2795 tmp1 = LIST_FIRST_ENTRY(list1, struct ice_vsig_prof, list); in ice_match_prop_lst()
2802 if (tmp2->profile_cookie != tmp1->profile_cookie) in ice_match_prop_lst()
2805 tmp1 = LIST_NEXT_ENTRY(tmp1, struct ice_vsig_prof, list); in ice_match_prop_lst()
6082 struct ice_vsig_prof *tmp1, *del1; in ice_add_prof_id_flow() local
6206 LIST_FOR_EACH_ENTRY_SAFE(del1, tmp1, &union_lst, ice_vsig_prof, list) { in ice_add_prof_id_flow()
6249 struct ice_vsig_prof *tmp1, *del1; in ice_rem_prof_id_flow() local
6360 LIST_FOR_EACH_ENTRY_SAFE(del1, tmp1, &copy, ice_vsig_prof, list) { in ice_rem_prof_id_flow()
/dpdk/drivers/net/bnx2x/
H A Delink.c8330 uint16_t val = 0, tmp1; in elink_8073_config_init() local
8430 tmp1 |= 1; in elink_8073_config_init()
8432 tmp1 &= 0xfffe; in elink_8073_config_init()
8435 tmp1 &= 0xfffe; in elink_8073_config_init()
8443 (tmp1 | ((phy->req_duplex == DUPLEX_FULL) ? in elink_8073_config_init()
8460 tmp1 |= (1 << 15); in elink_8073_config_init()
9880 uint16_t cnt, val, tmp1; in elink_8706_config_init() local
9973 tmp1 |= 0x1; in elink_8706_config_init()
10223 uint16_t tmp1, val; in elink_8727_config_speed() local
10234 ELINK_DEBUG_P1(sc, "1.7 = 0x%x", tmp1); in elink_8727_config_speed()
[all …]