Home
last modified time | relevance | path

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

12

/f-stack/freebsd/crypto/aesni/
H A Daesni_ghash.c197 tmp1 = _mm_xor_si128(tmp1, H2); in reduce4()
361 tmp1 = _mm_xor_si128(X, tmp1); in AES_GCM_encrypt()
438 tmp1 = _mm_xor_si128(tmp1, in AES_GCM_encrypt()
473 tmp1 = _mm_xor_si128(X, tmp1); in AES_GCM_encrypt()
490 tmp1 = _mm_xor_si128(tmp1, in AES_GCM_encrypt()
507 tmp1 = _mm_xor_si128(tmp1, in AES_GCM_encrypt()
622 tmp1 = _mm_xor_si128(X, tmp1); in AES_GCM_decrypt()
654 tmp1 = _mm_xor_si128(X, tmp1); in AES_GCM_decrypt()
742 tmp1 = _mm_xor_si128(tmp1, in AES_GCM_decrypt()
787 tmp1 = _mm_xor_si128(tmp1, in AES_GCM_decrypt()
[all …]
H A Daesni_wrap.c210 __m128i tmp1, tmp2, tmp3, tmp4; in aesni_encrypt_icm() local
227 tmp1 = _mm_shuffle_epi8(ctr1, BSWAP_EPI64); in aesni_encrypt_icm()
246 aesni_enc8(rounds - 1, key_schedule, tmp1, tmp2, tmp3, tmp4, in aesni_encrypt_icm()
264 tmp1 = _mm_shuffle_epi8(ctr1, BSWAP_EPI64); in aesni_encrypt_icm()
267 tot = aesni_enc(rounds - 1, key_schedule, tmp1); in aesni_encrypt_icm()
278 tmp1 = _mm_shuffle_epi8(ctr1, BSWAP_EPI64); in aesni_encrypt_icm()
279 tot = aesni_enc(rounds - 1, key_schedule, tmp1); in aesni_encrypt_icm()
/f-stack/dpdk/lib/librte_net/
H A Dnet_crc_sse.c71 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_128_to_64() local
75 tmp1 = _mm_srli_si128(data128, 8); in crcr32_reduce_128_to_64()
76 tmp0 = _mm_xor_si128(tmp0, tmp1); in crcr32_reduce_128_to_64()
80 tmp1 = _mm_clmulepi64_si128(tmp2, precomp, 0x10); in crcr32_reduce_128_to_64()
82 return _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_128_to_64()
107 __m128i tmp0, tmp1, tmp2; in crcr32_reduce_64_to_32() local
111 tmp1 = _mm_clmulepi64_si128(tmp0, precomp, 0x00); in crcr32_reduce_64_to_32()
112 tmp1 = _mm_xor_si128(tmp1, tmp0); in crcr32_reduce_64_to_32()
113 tmp1 = _mm_and_si128(tmp1, _mm_load_si128((const __m128i *)mask1)); in crcr32_reduce_64_to_32()
115 tmp2 = _mm_clmulepi64_si128(tmp1, precomp, 0x10); in crcr32_reduce_64_to_32()
[all …]
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_avx512.c54 __m512i tmp0, tmp1; in crcr32_folding_round() local
57 tmp1 = _mm512_clmulepi64_epi128(fold, precomp, 0x10); in crcr32_folding_round()
68 __m512i tmp0, tmp1, tmp2, tmp3; in crc32_fold_128() local
80 tmp0 = _mm512_ternarylogic_epi64(tmp0, tmp1, tmp2, 0x96); in crc32_fold_128()
83 tmp1 = _mm512_shuffle_i64x2(tmp0, tmp0, 0x4e); in crc32_fold_128()
146 __m128i tmp0, tmp1; in barrett_reduction() local
150 tmp1 = data64; in barrett_reduction()
156 tmp1 = data64; in barrett_reduction()
167 __m128i tmp, tmp1; in reduction_loop() local
172 tmp1 = _mm_loadu_si128((const __m128i *)&data[*n]); in reduction_loop()
[all …]
/f-stack/freebsd/arm64/arm64/
H A Dmemmove.S69 #define tmp1 x5 macro
79 #define E_h tmp1
93 sub tmp1, dstin, src
95 ccmp tmp1, count, 2, hi
98 cbz tmp1, 3f
107 and tmp1, dstend, 15
109 sub srcend, srcend, tmp1
110 sub count, count, tmp1
116 sub dstend, dstend, tmp1
H A Dmemcpy.S85 #define tmp1 x9 macro
108 sub tmp1, count, 1
110 tbnz tmp1, 6, L(copy96)
112 tbz tmp1, 5, 1f
145 lsr tmp1, count, 1
148 ldrb B_lw, [src, tmp1]
150 strb B_lw, [dstin, tmp1]
178 and tmp1, dstin, 15
181 sub src, src, tmp1
182 add count, count, tmp1 /* Count is now 16 too large. */
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_scalarmult/curve25519/ref10/
H A Dx25519_ref10.c64 fe25519 tmp1; in crypto_scalarmult_curve25519_ref10() local
93 fe25519_sub(tmp1, x2, z2); in crypto_scalarmult_curve25519_ref10()
97 fe25519_mul(z2, z2, tmp1); in crypto_scalarmult_curve25519_ref10()
98 fe25519_sq(tmp0, tmp1); in crypto_scalarmult_curve25519_ref10()
99 fe25519_sq(tmp1, x2); in crypto_scalarmult_curve25519_ref10()
102 fe25519_mul(x2, tmp1, tmp0); in crypto_scalarmult_curve25519_ref10()
103 fe25519_sub(tmp1, tmp1, tmp0); in crypto_scalarmult_curve25519_ref10()
105 fe25519_scalar_product(z3, tmp1, 121666); in crypto_scalarmult_curve25519_ref10()
109 fe25519_mul(z2, tmp1, tmp0); in crypto_scalarmult_curve25519_ref10()
/f-stack/freebsd/contrib/ipfilter/netinet/
H A Dipf_rb.h40 _t *parent, *tmp1, *tmp2; \
43 tmp1 = node->_f.right; \
44 tmp2 = tmp1->_f.left; \
51 parent->_f.right = tmp1; \
53 parent->_f.left = tmp1; \
54 tmp1->_f.left = node; \
56 node->_f.parent = tmp1; \
65 tmp1 = node->_f.left; \
66 tmp2 = tmp1->_f.right; \
73 parent->_f.right = tmp1; \
[all …]
/f-stack/freebsd/contrib/openzfs/lib/libzutil/os/linux/
H A Dzutil_device_path_os.c353 char *tmp1 = NULL; in zfs_get_enclosure_sysfs_path() local
364 tmp1 = strrchr(dev_name, '/'); in zfs_get_enclosure_sysfs_path()
365 if (tmp1 != NULL) in zfs_get_enclosure_sysfs_path()
366 dev_name = tmp1 + 1; /* +1 since we want the chr after '/' */ in zfs_get_enclosure_sysfs_path()
368 tmpsize = asprintf(&tmp1, "/sys/block/%s/device", dev_name); in zfs_get_enclosure_sysfs_path()
369 if (tmpsize == -1 || tmp1 == NULL) { in zfs_get_enclosure_sysfs_path()
370 tmp1 = NULL; in zfs_get_enclosure_sysfs_path()
374 dp = opendir(tmp1); in zfs_get_enclosure_sysfs_path()
376 tmp1 = NULL; /* To make free() at the end a NOP */ in zfs_get_enclosure_sysfs_path()
389 if (asprintf(&tmp2, "%s/%s", tmp1, ep->d_name) == -1 || in zfs_get_enclosure_sysfs_path()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-avx2.h81 __m256i tmp1 = _mm256_blend_epi32(B0, B1, 0xCC); \
83 B1 = _mm256_permute4x64_epi64(tmp1, _MM_SHUFFLE(2,3,0,1)); \
86 tmp1 = C0; \
88 C1 = tmp1; \
90 tmp1 = _mm256_blend_epi32(D0, D1, 0xCC); \
92 D0 = _mm256_permute4x64_epi64(tmp1, _MM_SHUFFLE(2,3,0,1)); \
109 __m256i tmp1 = _mm256_blend_epi32(B0, B1, 0xCC); \
111 B0 = _mm256_permute4x64_epi64(tmp1, _MM_SHUFFLE(2,3,0,1)); \
114 tmp1 = C0; \
116 C1 = tmp1; \
[all …]
/f-stack/freebsd/mips/cavium/cryptocteon/
H A Dcavium_crypto.c530 CVMX_MF_HSH_IV(tmp1, 0); in octo_null_sha1_encrypt()
540 CVMX_MT_HSH_DAT(tmp1, 0); in octo_null_sha1_encrypt()
554 CVMX_MF_HSH_IV(tmp1, 1); in octo_null_sha1_encrypt()
702 CVMX_MF_HSH_IV(tmp1, 0); in octo_aes_cbc_sha1_encrypt()
712 CVMX_MT_HSH_DAT(tmp1, 0); in octo_aes_cbc_sha1_encrypt()
743 CVMX_MF_HSH_IV(tmp1, 0); in octo_aes_cbc_sha1_encrypt()
748 CVMX_MF_HSH_IV(tmp1, 1); in octo_aes_cbc_sha1_encrypt()
893 CVMX_MF_HSH_IV(tmp1, 0); in octo_aes_cbc_sha1_decrypt()
903 CVMX_MT_HSH_DAT(tmp1, 0); in octo_aes_cbc_sha1_decrypt()
934 CVMX_MF_HSH_IV(tmp1, 0); in octo_aes_cbc_sha1_decrypt()
[all …]
/f-stack/dpdk/lib/librte_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()
/f-stack/dpdk/app/test/
H A Dtest_ipsec_sad.c420 uint64_t tmp1, tmp2, tmp3; in __test_lookup_adv() local
447 install_sa = &tmp1; in __test_lookup_adv()
454 RTE_TEST_ASSERT(sa[0] == &tmp1, in __test_lookup_adv()
456 RTE_TEST_ASSERT(sa[1] == &tmp1, in __test_lookup_adv()
458 RTE_TEST_ASSERT(sa[2] == &tmp1, in __test_lookup_adv()
507 install_sa = &tmp1; in __test_lookup_adv()
533 install_sa = &tmp1; in __test_lookup_adv()
588 install_sa = &tmp1; in __test_lookup_adv()
685 uint64_t tmp1, tmp2, tmp3; in __test_lookup_order() local
700 install_sa = &tmp1; in __test_lookup_order()
[all …]
/f-stack/dpdk/lib/librte_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 …]
/f-stack/freebsd/contrib/octeon-sdk/
H A Dcvmx-helper-ilk.c98 static cvmx_ilk_chan_pknd_t *chpknd = NULL, *tmp1; in __cvmx_helper_ilk_probe() local
185 tmp1 = chpknd; in __cvmx_helper_ilk_probe()
188 tmp1->chan = cvmx_ilk_chan_map[interface][j]; in __cvmx_helper_ilk_probe()
189 tmp1->pknd = i++; in __cvmx_helper_ilk_probe()
190 tmp1++; in __cvmx_helper_ilk_probe()
221 tmp1 = chpknd; in __cvmx_helper_ilk_probe()
225 tmp2->pipe_bpid = tmp1->pknd; in __cvmx_helper_ilk_probe()
227 tmp1++; in __cvmx_helper_ilk_probe()
H A Dcvmx-access-native.h328 uint32_t tmp1; \
345 : [tmp1] "=&r" (tmp1), [tmp2] "=&r" (tmp2), [tmp3] "=&r" (tmp3)\
354 uint32_t tmp1; \
366 : [tmp1] "=&r" (tmp1), [tmp2] "=&r" (tmp2) \
/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()
57 return (tmp1); 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()
89 return (tmp1); in ck_pr_cas_64_2()
H A Dck_pr_lse.h39 uint64_t tmp1; in ck_pr_cas_64_2_value() local
50 : "+&r" (x0), "+&r" (x1), "=&r" (tmp1), "=&r" (tmp2) in ck_pr_cas_64_2_value()
57 return (!!tmp1); in ck_pr_cas_64_2_value()
/f-stack/freebsd/contrib/ncsw/Peripherals/FM/MAC/
H A Dfman_tgec.c39 uint32_t tmp0, tmp1; in fman_tgec_set_mac_address() local
45 tmp1 = (uint32_t)(adr[4] | adr[5] << 8); in fman_tgec_set_mac_address()
47 iowrite32be(tmp1, &regs->mac_addr_1); in fman_tgec_set_mac_address()
257 uint32_t tmp0, tmp1; in fman_tgec_add_addr_in_paddr() local
263 tmp1 = (uint32_t)(adr[4] | adr[5] << 8); in fman_tgec_add_addr_in_paddr()
265 iowrite32be(tmp1, &regs->mac_addr_3); in fman_tgec_add_addr_in_paddr()
H A Dfman_memac.c82 uint32_t tmp0, tmp1; in fman_memac_add_addr_in_paddr() local
88 tmp1 = (uint32_t)(adr[4] | adr[5] << 8); in fman_memac_add_addr_in_paddr()
92 iowrite32be(tmp1, &regs->mac_addr0.mac_addr_u); in fman_memac_add_addr_in_paddr()
95 iowrite32be(tmp1, &regs->mac_addr[paddr_num-1].mac_addr_u); in fman_memac_add_addr_in_paddr()
H A Dfman_dtsec.c369 uint32_t tmp1, tmp2; in fman_dtsec_get_mac_address() local
371 tmp1 = ioread32be(&regs->macstnaddr1); in fman_dtsec_get_mac_address()
376 macaddr[2] = (uint8_t)(tmp1 & 0x000000ff); in fman_dtsec_get_mac_address()
377 macaddr[3] = (uint8_t)((tmp1 & 0x0000ff00) >> 8); in fman_dtsec_get_mac_address()
378 macaddr[4] = (uint8_t)((tmp1 & 0x00ff0000) >> 16); in fman_dtsec_get_mac_address()
379 macaddr[5] = (uint8_t)((tmp1 & 0xff000000) >> 24); in fman_dtsec_get_mac_address()
/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/drivers/net/bnxt/
H A Dbnxt_rxtx_vec_sse.c198 __m128i tmp0, tmp1, info3_v; in bnxt_recv_pkts_vec() local
204 tmp1 = _mm_loadu_si128((void *)&rxr->rx_buf_ring[mbcons + 2]); in bnxt_recv_pkts_vec()
208 _mm_storeu_si128((void *)&rx_pkts[i + 2], tmp1); in bnxt_recv_pkts_vec()
229 tmp1 = _mm_unpackhi_epi32(rxcmp1[2], rxcmp1[3]); in bnxt_recv_pkts_vec()
242 info3_v = _mm_and_si128(_mm_unpacklo_epi64(tmp0, tmp1), in bnxt_recv_pkts_vec()

12