| /dpdk/lib/net/ |
| H A D | net_crc_sse.c | 70 __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 D | net_crc_neon.c | 70 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
80 tmp2 = vshift_bytes_left(tmp0, 4); in crcr32_reduce_128_to_64()
82 vgetq_lane_p64(vreinterpretq_p64_u64(tmp2), 0), in crcr32_reduce_128_to_64()
106 uint64x2_t tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
116 tmp2 = vreinterpretq_u64_p128(vmull_p64( in crcr32_reduce_64_to_32()
119 tmp2 = veorq_u64(tmp2, tmp1); in crcr32_reduce_64_to_32()
120 tmp2 = veorq_u64(tmp2, tmp0); in crcr32_reduce_64_to_32()
122 return vgetq_lane_u32(vreinterpretq_u32_u64(tmp2), 2); in crcr32_reduce_64_to_32()
|
| H A D | net_crc_avx512.c | 65 __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/lib/fib/ |
| H A D | trie_avx512.c | 15 __m512i tmp1, tmp2, tmp3, tmp4; in transpose_x16() local
25 tmp2 = _mm512_loadu_si512(&ips[4]); 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]); in transpose_x8()
63 tmp3 = _mm512_unpacklo_epi64(tmp1, tmp2); in transpose_x8()
65 tmp4 = _mm512_unpackhi_epi64(tmp1, tmp2); in transpose_x8()
[all...] |
| H A D | dir24_8_avx512.c | 22 __m512i tmp1, tmp2, res_msk; in dir24_8_vec_lookup_x16() local
83 tmp2 = _mm512_maskz_expand_epi32(exp_msk, in dir24_8_vec_lookup_x8_8b()
86 _mm512_storeu_si512(next_hops + 8, tmp2); in dir24_8_vec_lookup_x8_8b()
|
| /dpdk/app/test/ |
| H A D | test_cmdline_cirbuf.c | 479 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/bpf/ |
| H A D | bpf_jit_arm64.c | 1021 emit_xadd(struct a64_jit_ctx *ctx, uint8_t op, uint8_t tmp1, uint8_t tmp2, in emit_xadd() argument
1038 emit_ldxr(ctx, is64, tmp2, rn); in emit_xadd()
1039 emit_add(ctx, is64, tmp2, src); in emit_xadd()
1040 emit_stxr(ctx, is64, tmp3, tmp2, rn); in emit_xadd()
1119 uint8_t op, dst, src, tmp1, tmp2, tmp3; in emit() local
1133 tmp2 = ebpf_to_a64_reg(ctx, TMP_REG_2); in emit()
1216 emit_mod(ctx, is64, tmp2, dst, tmp1); in emit()
1322 emit_mov_imm(ctx, 1, tmp2, off); in emit()
1323 emit_str(ctx, BPF_SIZE(op), tmp1, dst, tmp2); in emit()
1328 emit_xadd(ctx, op, tmp1, tmp2, tmp3, dst, off, src); in emit()
|
| /dpdk/drivers/net/qede/base/ |
| H A D | ecore_int.c | 240 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/bnx2x/ |
| H A D | elink.c | 10294 uint16_t tmp1, mod_abs, tmp2; in elink_8727_config_init() local
10359 MDIO_PMA_DEVAD, MDIO_PMA_REG_8727_OPT_CFG_REG, &tmp2); in elink_8727_config_init()
10360 tmp2 |= 0x1000; in elink_8727_config_init()
10361 tmp2 &= 0xFFEF; in elink_8727_config_init()
10363 MDIO_PMA_DEVAD, MDIO_PMA_REG_8727_OPT_CFG_REG, tmp2); in elink_8727_config_init()
10366 &tmp2); in elink_8727_config_init()
10369 (tmp2 & 0x7fff)); in elink_8727_config_init()
|