Searched refs:b0 (Results 1 - 25 of 76) sorted by relevance

1234

/freebsd-13-stable/sys/contrib/libb2/
H A Dblake2b-load-sse2.h17 #define LOAD_MSG_0_1(b0, b1) b0 = _mm_set_epi64x(m2, m0); b1 = _mm_set_epi64x(m6, m4)
18 #define LOAD_MSG_0_2(b0, b1) b0 = _mm_set_epi64x(m3, m1); b1 = _mm_set_epi64x(m7, m5)
19 #define LOAD_MSG_0_3(b0, b1) b0 = _mm_set_epi64x(m10, m8); b1 = _mm_set_epi64x(m14, m12)
20 #define LOAD_MSG_0_4(b0, b1) b0 = _mm_set_epi64x(m11, m9); b1 = _mm_set_epi64x(m15, m13)
21 #define LOAD_MSG_1_1(b0, b1) b0
[all...]
H A Dblake2b-load-sse41.h17 #define LOAD_MSG_0_1(b0, b1) \
20 b0 = _mm_unpacklo_epi64(m0, m1); \
25 #define LOAD_MSG_0_2(b0, b1) \
28 b0 = _mm_unpackhi_epi64(m0, m1); \
33 #define LOAD_MSG_0_3(b0, b1) \
36 b0 = _mm_unpacklo_epi64(m4, m5); \
41 #define LOAD_MSG_0_4(b0, b1) \
44 b0 = _mm_unpackhi_epi64(m4, m5); \
49 #define LOAD_MSG_1_1(b0, b1) \
52 b0
[all...]
H A Dblake2b-round.h47 #define G1(row1l,row2l,row3l,row4l,row1h,row2h,row3h,row4h,b0,b1) \
48 row1l = _mm_add_epi64(_mm_add_epi64(row1l, b0), row2l); \
66 #define G2(row1l,row2l,row3l,row4l,row1h,row2h,row3h,row4h,b0,b1) \
67 row1l = _mm_add_epi64(_mm_add_epi64(row1l, b0), row2l); \
148 LOAD_MSG_ ##r ##_1(b0, b1); \
149 G1(row1l,row2l,row3l,row4l,row1h,row2h,row3h,row4h,b0,b1); \
150 LOAD_MSG_ ##r ##_2(b0, b1); \
151 G2(row1l,row2l,row3l,row4l,row1h,row2h,row3h,row4h,b0,b1); \
153 LOAD_MSG_ ##r ##_3(b0, b1); \
154 G1(row1l,row2l,row3l,row4l,row1h,row2h,row3h,row4h,b0,b
[all...]
/freebsd-13-stable/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-load-sse2.h19 #define LOAD_MSG_0_1(b0, b1) \
20 b0 = _mm_set_epi64x(m2, m0); \
22 #define LOAD_MSG_0_2(b0, b1) \
23 b0 = _mm_set_epi64x(m3, m1); \
25 #define LOAD_MSG_0_3(b0, b1) \
26 b0 = _mm_set_epi64x(m10, m8); \
28 #define LOAD_MSG_0_4(b0, b1) \
29 b0 = _mm_set_epi64x(m11, m9); \
31 #define LOAD_MSG_1_1(b0, b1) \
32 b0
[all...]
H A Dblake2b-load-sse41.h19 #define LOAD_MSG_0_1(b0, b1) \
21 b0 = _mm_unpacklo_epi64(m0, m1); \
25 #define LOAD_MSG_0_2(b0, b1) \
27 b0 = _mm_unpackhi_epi64(m0, m1); \
31 #define LOAD_MSG_0_3(b0, b1) \
33 b0 = _mm_unpacklo_epi64(m4, m5); \
37 #define LOAD_MSG_0_4(b0, b1) \
39 b0 = _mm_unpackhi_epi64(m4, m5); \
43 #define LOAD_MSG_1_1(b0, b1) \
45 b0
[all...]
H A Dblake2b-load-avx2.h4 #define BLAKE2B_LOAD_MSG_0_1(b0) \
8 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
11 #define BLAKE2B_LOAD_MSG_0_2(b0) \
15 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
18 #define BLAKE2B_LOAD_MSG_0_3(b0) \
22 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
25 #define BLAKE2B_LOAD_MSG_0_4(b0) \
29 b0 = _mm256_blend_epi32(t0, t1, 0xF0); \
32 #define BLAKE2B_LOAD_MSG_1_1(b0) \
36 b0
[all...]
H A Dblake2b-compress-sse41.h21 #define G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \
22 row1l = _mm_add_epi64(_mm_add_epi64(row1l, b0), row2l); \
40 #define G2(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \
41 row1l = _mm_add_epi64(_mm_add_epi64(row1l, b0), row2l); \
92 LOAD_MSG_##r##_1(b0, b1); \
93 G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1); \
94 LOAD_MSG_##r##_2(b0, b1); \
95 G2(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1); \
97 LOAD_MSG_##r##_3(b0, b1); \
98 G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b
[all...]
H A Dblake2b-compress-ssse3.h21 #define G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \
22 row1l = _mm_add_epi64(_mm_add_epi64(row1l, b0), row2l); \
40 #define G2(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \
41 row1l = _mm_add_epi64(_mm_add_epi64(row1l, b0), row2l); \
92 LOAD_MSG_##r##_1(b0, b1); \
93 G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1); \
94 LOAD_MSG_##r##_2(b0, b1); \
95 G2(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1); \
97 LOAD_MSG_##r##_3(b0, b1); \
98 G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b
[all...]
H A Dblake2b-compress-avx2.h82 __m256i b0; \
83 BLAKE2B_LOAD_MSG_##r##_1(b0); \
84 BLAKE2B_G1_V1(a, b, c, d, b0); \
85 BLAKE2B_LOAD_MSG_##r##_2(b0); \
86 BLAKE2B_G2_V1(a, b, c, d, b0); \
88 BLAKE2B_LOAD_MSG_##r##_3(b0); \
89 BLAKE2B_G1_V1(a, b, c, d, b0); \
90 BLAKE2B_LOAD_MSG_##r##_4(b0); \
91 BLAKE2B_G2_V1(a, b, c, d, b0); \
/freebsd-13-stable/contrib/googletest/googletest/test/
H A Dgoogletest-linked-ptr-test.cc100 linked_ptr<B> b0(new B);
101 linked_ptr<A> a6(b0);
102 ASSERT_TRUE(b0 == a6);
103 ASSERT_TRUE(a6 == b0);
104 ASSERT_TRUE(b0 != NULL);
105 a5 = b0;
106 a5 = b0;
111 b0->Use();
112 (*b0).Use();
113 b0
[all...]
/freebsd-13-stable/sys/cddl/boot/zfs/
H A Dfletcher.c32 uint64_t a0, b0, a1, b1; local
34 for (a0 = b0 = a1 = b1 = 0; ip < ipend; ip += 2) {
37 b0 += a0;
41 ZIO_SET_CHECKSUM(zcp, a0, a1, b0, b1);
50 uint64_t a0, b0, a1, b1; local
52 for (a0 = b0 = a1 = b1 = 0; ip < ipend; ip += 2) {
55 b0 += a0;
59 ZIO_SET_CHECKSUM(zcp, a0, a1, b0, b1);
/freebsd-13-stable/contrib/libpcap/
H A Dgencode.c914 * Merge the lists in b0 and b1, using the 'sense' field to indicate
918 merge(struct block *b0, struct block *b1) argument
920 register struct block **p = &b0;
988 gen_and(struct block *b0, struct block *b1) argument
990 backpatch(b0, b1->head);
991 b0->sense = !b0->sense;
993 merge(b1, b0);
995 b1->head = b0->head;
999 gen_or(struct block *b0, struc argument
1961 struct block *b0, *b1; local
2199 struct block *b0, *b1; local
3092 struct block *b0; local
3138 struct block *b0, *b1, *b2; local
3678 struct block *b0, *b1; local
3763 struct block *b0, *b1; local
3794 struct block *b0, *b1; local
3820 struct block *b0, *b1; local
3846 struct block *b0, *b1; local
3871 struct block *b0, *b1; local
3984 struct block *b0, *b1; local
4049 struct block *b0, *b1; local
4123 register struct block *b0, *b1; local
4179 struct block *b0, *b1; local
4235 register struct block *b0, *b1; local
4292 register struct block *b0, *b1, *b2; local
4716 register struct block *b0, *b1; local
4787 struct block *b0, *b1, *b2, *tmp; local
4883 struct block *b0, *b1; local
4912 struct block *b0, *b1; local
5205 struct block *b0, *b1, *tmp; local
5310 struct block *b0; local
5600 struct block *b0, *b1, *tmp; local
5665 struct block *b0, *b1, *tmp; local
5711 struct block *b0, *b1, *tmp; local
5750 struct block *b0, *b1, *tmp; local
5807 struct block *b0, *b1, *tmp; local
5873 struct block *b0, *b1, *tmp; local
5929 struct block *b0, *b1, *tmp; local
5969 struct block *b0, *b1, *tmp; local
6342 struct block *b0, *b1; local
6376 struct block *b0, *b1; local
7922 struct block *b0, *b1, *b2; local
7993 register struct block *b0; local
8007 register struct block *b0, *b1, *b2; local
8200 register struct block *b0; local
8350 struct block *b0; local
8380 struct block *b0; local
8409 struct block *b0; local
8432 struct block *b0; local
8455 struct block *b0; local
8478 struct block *b0; local
8586 struct block *b0; local
8616 struct block *b0; local
8682 register struct block *b0, *b1; local
8736 struct block *b0, *b1; local
8763 struct block *b0, *b1; local
8878 struct block *b0, *b_tpid, *b_vid = NULL; local
8924 struct block *b0; local
9024 struct block *b0, *b1; local
9118 struct block *b0, *b1; local
9182 struct block *b0, *b1; local
9216 struct block *b0, *b1; local
9242 struct block *b0, *b1; local
9420 struct block *b0, *b1; local
9457 struct block *b0; local
9485 struct block *b0; local
9539 struct block *b0, *b1; local
9550 struct block *b0, *b1; local
9561 struct block *b0; local
9586 struct block *b0, *b1; local
9693 struct block *b0, *b1; local
9774 struct block *b0; local
9923 struct block *b0, *b1; local
[all...]
/freebsd-13-stable/contrib/netbsd-tests/lib/libc/string/
H A Dt_memmem.c57 char b0[] = ""; variable
82 expect(memmem(b0, lb0, p0, lp0) == NULL);
85 expect(memmem(b0, lb0, p0, lp0) == b0);
87 expect(memmem(b0, lb0, p1, lp1) == NULL);
/freebsd-13-stable/sys/dev/usb/
H A Dusb_endian.h100 #define USETW2(w,b1,b0) do { \
101 (w)[0] = (uint8_t)(b0); \
105 #define USETW4(w,b3,b2,b1,b0) do { \
106 (w)[0] = (uint8_t)(b0); \
112 #define USETW8(w,b7,b6,b5,b4,b3,b2,b1,b0) do { \
113 (w)[0] = (uint8_t)(b0); \
/freebsd-13-stable/sys/net80211/
H A Dieee80211_crypto_ccmp.c222 READ_6(uint8_t b0, uint8_t b1, uint8_t b2, uint8_t b3, uint8_t b4, uint8_t b5) argument
224 uint32_t iv32 = (b0 << 0) | (b1 << 8) | (b2 << 16) | (b3 << 24);
347 uint8_t b0[AES_BLOCK_LEN], uint8_t aad[2 * AES_BLOCK_LEN],
357 b0[0] = 0x59;
358 /* NB: b0[1] set below */
359 IEEE80211_ADDR_COPY(b0 + 2, wh->i_addr2);
360 b0[8] = pn >> 40;
361 b0[9] = pn >> 32;
362 b0[10] = pn >> 24;
363 b0[1
345 ccmp_init_blocks(rijndael_ctx *ctx, struct ieee80211_frame *wh, u_int64_t pn, size_t dlen, uint8_t b0[AES_BLOCK_LEN], uint8_t aad[2 * AES_BLOCK_LEN], uint8_t auth[AES_BLOCK_LEN], uint8_t s0[AES_BLOCK_LEN]) argument
456 uint8_t aad[2 * AES_BLOCK_LEN], b0[AES_BLOCK_LEN], b[AES_BLOCK_LEN], local
601 uint8_t b0[AES_BLOCK_LEN], b[AES_BLOCK_LEN], a[AES_BLOCK_LEN]; local
[all...]
/freebsd-13-stable/contrib/bearssl/src/int/
H A Di32_muladd.c33 uint32_t a0, a1, b0, hi, g, q, tb; local
58 * b = b0 * w^N + b2
63 * w/2 <= b0 < w
67 * b0, we ensured that b0 is "full" (high bit set), and a is
72 * a0*w+a1 = b0*u + v (with 0 <= v < w)
82 b0 = br_i32_word(m, m_bitlen - 32);
87 * -- If a0 == b0 then g == 0; we want q = 0xFFFFFFFF.
94 g = br_div(a0, a1, b0);
95 q = MUX(EQ(a0, b0),
[all...]
H A Di31_muladd.c34 uint32_t a0, a1, b0, hi, g, q, tb; local
64 * b = b0 * w^N + b2
69 * w/2 <= b0 < w
73 * b0, we ensured that b0 is "full" (high bit set), and a is
78 * a0*w+a1 = b0*u + v (with 0 <= v < b0)
89 b0 = m[mlen];
97 b0 = ((m[mlen] << (31 - mblr)) | (m[mlen - 1] >> mblr))
104 * -- If a0 == b0 the
[all...]
/freebsd-13-stable/usr.sbin/diskinfo/
H A Ddiskinfo.c412 off_t b0, b1, sectorcount, step; local
432 b0 = 0;
436 rdsect(fd, b0, sectorsize);
437 b0 += step;
444 b0 = sectorcount / 4;
445 b1 = b0 + sectorcount / 2;
448 rdsect(fd, b0, sectorsize);
449 b0 += step;
455 b0 = sectorcount / 4;
456 b1 = b0
[all...]
/freebsd-13-stable/contrib/llvm-project/llvm/lib/CodeGen/
H A DEdgeBundles.cpp62 unsigned b0 = getBundle(i, false); local
64 Blocks[b0].push_back(i);
65 if (b1 != b0)
/freebsd-13-stable/sys/opencrypto/
H A Dcbc_mac.c88 uint8_t b0[CCM_CBC_BLOCK_LEN]; local
89 uint8_t *bp = b0, flags = 0;
118 b0[0] = flags;
119 bcopy(nonce, b0 + 1, nonceLen);
120 bp = b0 + 1 + nonceLen;
123 for (uint8_t *dst = b0 + sizeof(b0) - 1; dst >= bp; dst--) {
127 /* Now need to encrypt b0 */
128 rijndaelEncrypt(ctx->keysched, ctx->rounds, b0, ctx->block);
/freebsd-13-stable/contrib/bearssl/src/symcipher/
H A Dchacha20_sse2.c199 __m128i b0, b1, b2, b3; local
201 b0 = _mm_loadu_si128((const void *)(buf + 0));
205 b0 = _mm_xor_si128(b0, s0);
209 _mm_storeu_si128((void *)(buf + 0), b0);
/freebsd-13-stable/tools/tools/ath/athkey/
H A Dathkey.c61 int b0, b1; local
71 b0 = toint(cp[0]);
81 b1 = b0, b0 = 0;
89 data[len++] = (b0<<4) | b1;
/freebsd-13-stable/sys/contrib/libsodium/src/libsodium/crypto_stream/salsa20/xmm6int/
H A Du0.h7 __m128i b0, b1, b2, b3, b4, b5, b6, b7; variable
16 b0 = a0;
18 b0 = _mm_srli_epi32(b0, 25);
21 diag3 = _mm_xor_si128(diag3, b0);
88 b0 = a0;
90 b0 = _mm_srli_epi32(b0, 25);
93 diag3 = _mm_xor_si128(diag3, b0);
H A Du1.h7 __m128i b0, b1, b2, b3, b4, b5, b6, b7; variable
17 b0 = a0;
19 b0 = _mm_srli_epi32(b0, 25);
22 diag3 = _mm_xor_si128(diag3, b0);
89 b0 = a0;
91 b0 = _mm_srli_epi32(b0, 25);
94 diag3 = _mm_xor_si128(diag3, b0);
/freebsd-13-stable/crypto/openssl/crypto/chacha/asm/
H A Dchacha-c64xplus.pl122 my ($b0,$b1,$b2,$b3) = (4..7);
130 || ADD @X[$b0],@X[$a0],@X[$a0]
153 || XOR @X[$c0],@X[$b0],@X[$b0]
161 ROTL @X[$b0],12,@X[$b0]
165 ADD @Y[$b0],@Y[$a0],@Y[$a0]
174 || ADD @X[$b0],@X[$a0],@X[$a0]
198 || XOR @Y[$c0],@Y[$b0],@Y[$b0]
[all...]

Completed in 221 milliseconds

1234