Home
last modified time | relevance | path

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

12

/f-stack/freebsd/crypto/aesni/
H A Daesni_ghash.c150 tmp2 = _mm_xor_si128(tmp2, tmp4); in gfmul()
151 tmp2 = _mm_xor_si128(tmp2, tmp5); in gfmul()
152 tmp2 = _mm_xor_si128(tmp2, tmp8); in gfmul()
201 tmp2 = _mm_xor_si128(tmp2, H3); in reduce4()
253 tmp2 = _mm_xor_si128(tmp2, tmp4); in reduce4()
254 tmp2 = _mm_xor_si128(tmp2, tmp5); in reduce4()
255 tmp2 = _mm_xor_si128(tmp2, tmp8); in reduce4()
411 tmp2 =_mm_xor_si128(tmp2, KEY[0]); in AES_GCM_encrypt()
440 tmp2 = _mm_xor_si128(tmp2, in AES_GCM_encrypt()
715 tmp2 =_mm_xor_si128(tmp2, KEY[0]); in AES_GCM_decrypt()
[all …]
/f-stack/dpdk/lib/librte_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()
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()
160 tmp2 = _mm512_maskz_expand_epi32(exp_msk, in trie_vec_lookup_x16()
[all …]
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()
/f-stack/dpdk/lib/librte_net/
H A Dnet_crc_sse.c71 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
79 tmp2 = _mm_slli_si128(tmp0, 4); in crcr32_reduce_128_to_64()
80 tmp1 = _mm_clmulepi64_si128(tmp2, precomp, 0x10); in crcr32_reduce_128_to_64()
107 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
115 tmp2 = _mm_clmulepi64_si128(tmp1, precomp, 0x10); in crcr32_reduce_64_to_32()
116 tmp2 = _mm_xor_si128(tmp2, tmp1); in crcr32_reduce_64_to_32()
117 tmp2 = _mm_xor_si128(tmp2, tmp0); in crcr32_reduce_64_to_32()
119 return _mm_extract_epi32(tmp2, 2); in crcr32_reduce_64_to_32()
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_avx512.c68 __m512i tmp0, tmp1, tmp2, tmp3; in crc32_fold_128() local
77 tmp2 = _mm512_clmulepi64_epi128(fold1, params->fold_3x128b, 0x01); in crc32_fold_128()
80 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp1, tmp2, 0x96); in crc32_fold_128()
/f-stack/freebsd/contrib/ipfilter/netinet/
H A Dipf_rb.h40 _t *parent, *tmp1, *tmp2; \
44 tmp2 = tmp1->_f.left; \
45 node->_f.right = tmp2; \
46 if (tmp2 != & _n##_rb_zero) \
47 tmp2->_f.parent = node; \
62 _t *parent, *tmp1, *tmp2; \
66 tmp2 = tmp1->_f.right; \
67 node->_f.left = tmp2; \
68 if (tmp2 != &_n##_rb_zero) \
69 tmp2->_f.parent = node; \
[all …]
/f-stack/freebsd/contrib/octeon-sdk/
H A Dcvmx-helper-ilk.c99 static cvmx_ilk_cal_entry_t *calent = NULL, *tmp2; in __cvmx_helper_ilk_probe() local
222 tmp2 = calent; in __cvmx_helper_ilk_probe()
225 tmp2->pipe_bpid = tmp1->pknd; in __cvmx_helper_ilk_probe()
226 tmp2->ent_ctrl = PIPE_BPID; in __cvmx_helper_ilk_probe()
228 tmp2++; in __cvmx_helper_ilk_probe()
244 tmp2 = calent; in __cvmx_helper_ilk_probe()
247 tmp2->pipe_bpid = tmp->pipe; in __cvmx_helper_ilk_probe()
248 tmp2->ent_ctrl = PIPE_BPID; in __cvmx_helper_ilk_probe()
250 tmp2++; in __cvmx_helper_ilk_probe()
H A Dcvmx-access-native.h329 uint32_t tmp2; \
345 : [tmp1] "=&r" (tmp1), [tmp2] "=&r" (tmp2), [tmp3] "=&r" (tmp3)\
355 uint32_t tmp2; \
366 : [tmp1] "=&r" (tmp1), [tmp2] "=&r" (tmp2) \
/f-stack/freebsd/contrib/libsodium/msvc-scripts/
H A Dprocess.bat2 cscript msvc-scripts/rep.vbs //Nologo s/@SODIUM_LIBRARY_VERSION_MAJOR@/10/ < tmp > tmp2
3 cscript msvc-scripts/rep.vbs //Nologo s/@SODIUM_LIBRARY_VERSION_MINOR@/1/ < tmp2 > tmp3
5 del tmp tmp2 tmp3
/f-stack/dpdk/app/test/
H A Dtest_ipsec_sad.c420 uint64_t tmp1, tmp2, tmp3; in __test_lookup_adv() local
467 install_sa = &tmp2; in __test_lookup_adv()
474 RTE_TEST_ASSERT(sa[0] == &tmp2, in __test_lookup_adv()
476 RTE_TEST_ASSERT(sa[1] == &tmp2, in __test_lookup_adv()
511 install_sa = &tmp2; in __test_lookup_adv()
518 RTE_TEST_ASSERT(sa[0] == &tmp2, in __test_lookup_adv()
559 install_sa = &tmp2; in __test_lookup_adv()
592 install_sa = &tmp2; in __test_lookup_adv()
685 uint64_t tmp1, tmp2, tmp3; in __test_lookup_order() local
715 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()
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-avx2.h82 __m256i tmp2 = _mm256_blend_epi32(B0, B1, 0x33); \
84 B0 = _mm256_permute4x64_epi64(tmp2, _MM_SHUFFLE(2,3,0,1)); \
91 tmp2 = _mm256_blend_epi32(D0, D1, 0x33); \
93 D1 = _mm256_permute4x64_epi64(tmp2, _MM_SHUFFLE(2,3,0,1)); \
110 __m256i tmp2 = _mm256_blend_epi32(B0, B1, 0x33); \
112 B1 = _mm256_permute4x64_epi64(tmp2, _MM_SHUFFLE(2,3,0,1)); \
119 tmp2 = _mm256_blend_epi32(D0, D1, 0xCC); \
121 D1 = _mm256_permute4x64_epi64(tmp2, _MM_SHUFFLE(2,3,0,1)); \
/f-stack/freebsd/contrib/openzfs/lib/libzutil/os/linux/
H A Dzutil_device_path_os.c354 char *tmp2 = NULL; in zfs_get_enclosure_sysfs_path() local
389 if (asprintf(&tmp2, "%s/%s", tmp1, ep->d_name) == -1 || in zfs_get_enclosure_sysfs_path()
390 tmp2 == NULL) in zfs_get_enclosure_sysfs_path()
393 size = readlink(tmp2, buf, sizeof (buf)); in zfs_get_enclosure_sysfs_path()
397 free(tmp2); in zfs_get_enclosure_sysfs_path()
398 tmp2 = NULL; /* To make free() at the end a NOP */ in zfs_get_enclosure_sysfs_path()
430 free(tmp2); in zfs_get_enclosure_sysfs_path()
/f-stack/freebsd/arm/include/
H A Datomic-v6.h95 uint32_t tmp = 0, tmp2 = 0; in atomic_add_32() local
104 : "=&r" (tmp), "+r" (tmp2) in atomic_add_32()
144 uint32_t tmp = 0, tmp2 = 0; in ATOMIC_ACQ_REL_LONG() local
153 : "=&r" (tmp), "+r" (tmp2), "+r" (address), "+r" (setmask) in ATOMIC_ACQ_REL_LONG()
573 uint32_t tmp = 0, tmp2 = 0, ret = 0; in atomic_fetchadd_32() local
670 uint32_t ret, tmp = 0, tmp2 = 0; in atomic_readandclear_32() local
679 : "=r" (ret), "=&r" (tmp), "+r" (tmp2), "+r" (p) in atomic_readandclear_32()
717 uint32_t tmp = 0, tmp2 = 0; in atomic_set_32() local
726 : "=&r" (tmp), "+r" (tmp2), "+r" (address), "+r" (setmask) in atomic_set_32()
766 uint32_t tmp = 0, tmp2 = 0; in ATOMIC_ACQ_REL_LONG() local
[all …]
/f-stack/freebsd/contrib/zstd/examples/
H A DMakefile70 cp Makefile tmp2
90 ./dictionary_compression tmp2 tmp README.md
91 ./dictionary_decompression tmp2.zst tmp.zst README.md
/f-stack/freebsd/arm/arm/
H A Dswtch-v6.S93 #define GET_PCPU(tmp, tmp2) \ argument
96 ldr tmp2, .Lcurpcpu+4; \
97 mul tmp, tmp, tmp2; \
98 ldr tmp2, .Lcurpcpu; \
99 add tmp, tmp, tmp2;
102 #define GET_PCPU(tmp, tmp2) \ argument
H A Dcpufunc.c305 uint32_t tmp, tmp2; in arm11x6_setup() local
322 tmp2 = tmp; in arm11x6_setup()
325 if (tmp != tmp2) in arm11x6_setup()
/f-stack/freebsd/contrib/openzfs/cmd/zed/
H A Dzed_disk_event.c163 char *tmp, *tmp2; in zed_udev_monitor() local
288 tmp2 = zfs_get_underlying_path(tmp); in zed_udev_monitor()
289 if (tmp && tmp2 && (strcmp(tmp, tmp2) != 0)) { in zed_udev_monitor()
313 free(tmp2); in zed_udev_monitor()
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_aead/aes256gcm/aesni/
H A Daead_aes256gcm_aesni.c205 __m128i tmp2, tmp3, tmp4, tmp5, tmp6, tmp7, tmp8, tmp9; in addmul() local
253 tmp2 = _mm_srli_epi32(tmp30, 1); in addmul()
256 tmp34 = _mm_xor_si128(tmp2, tmp12); in addmul()
295 __m128i tmp2 = _mm_srli_epi32(tmp30, 1); in mulv() local
298 __m128i tmp34 = _mm_xor_si128(tmp2, tmp12); in mulv()
372 tmp0 = _mm_xor_si128(tmp2, tmp0); \
400 tmp2 = _mm_srli_epi32(tmp3, 1); \
403 tmp2 = _mm_xor_si128(tmp2, tmp0B); \
404 tmp2 = _mm_xor_si128(tmp2, tmp1B); \
405 tmp2 = _mm_xor_si128(tmp2, tmp8); \
[all …]
/f-stack/freebsd/mips/cavium/cryptocteon/
H A Dcavium_crypto.c472 uint64_t tmp1, tmp2, tmp3; in octo_null_sha1_encrypt() local
531 CVMX_MF_HSH_IV(tmp2, 1); in octo_null_sha1_encrypt()
541 CVMX_MT_HSH_DAT(tmp2, 1); in octo_null_sha1_encrypt()
579 uint64_t tmp1, tmp2, tmp3; in octo_aes_cbc_sha1_encrypt() local
703 CVMX_MF_HSH_IV(tmp2, 1); in octo_aes_cbc_sha1_encrypt()
713 CVMX_MT_HSH_DAT(tmp2, 1); in octo_aes_cbc_sha1_encrypt()
770 uint64_t tmp1, tmp2, tmp3; in octo_aes_cbc_sha1_decrypt() local
894 CVMX_MF_HSH_IV(tmp2, 1); in octo_aes_cbc_sha1_decrypt()
904 CVMX_MT_HSH_DAT(tmp2, 1); in octo_aes_cbc_sha1_decrypt()
/f-stack/freebsd/contrib/ck/include/gcc/aarch64/
H A Dck_pr_llsc.h38 uint64_t tmp1, tmp2; in ck_pr_cas_64_2_value() local
53 : "=&r" (tmp1), "=&r" (tmp2), "=&r" (value[0]), "=&r" (value[1]) in ck_pr_cas_64_2_value()
72 uint64_t tmp1, tmp2; in ck_pr_cas_64_2() local
85 : "=&r" (tmp1), "=&r" (tmp2) in ck_pr_cas_64_2()
H A Dck_pr_lse.h40 uint64_t tmp2; in ck_pr_cas_64_2_value() local
50 : "+&r" (x0), "+&r" (x1), "=&r" (tmp1), "=&r" (tmp2) in ck_pr_cas_64_2_value()
/f-stack/freebsd/x86/x86/
H A Dpvclock.c92 uint32_t tmp1, tmp2; in pvclock_scale_delta() local
109 : "=A" (product), "=r" (tmp1), "=r" (tmp2) in pvclock_scale_delta()
/f-stack/dpdk/lib/librte_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()

12