Home
last modified time | relevance | path

Searched full:b1 (Results 1 – 25 of 760) sorted by relevance

12345678910>>...31

/freebsd/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) argument
18 #define LOAD_MSG_0_2(b0, b1) b0 = _mm_set_epi64x(m3, m1); b1 = _mm_set_epi64x(m7, m5) argument
19 #define LOAD_MSG_0_3(b0, b1) b0 = _mm_set_epi64x(m10, m8); b1 = _mm_set_epi64x(m14, m12) argument
20 #define LOAD_MSG_0_4(b0, b1) b0 = _mm_set_epi64x(m11, m9); b1 = _mm_set_epi64x(m15, m13) argument
21 #define LOAD_MSG_1_1(b0, b1) b0 = _mm_set_epi64x(m4, m14); b1 = _mm_set_epi64x(m13, m9) argument
22 #define LOAD_MSG_1_2(b0, b1) b0 = _mm_set_epi64x(m8, m10); b1 = _mm_set_epi64x(m6, m15) argument
23 #define LOAD_MSG_1_3(b0, b1) b0 = _mm_set_epi64x(m0, m1); b1 = _mm_set_epi64x(m5, m11) argument
24 #define LOAD_MSG_1_4(b0, b1) b0 = _mm_set_epi64x(m2, m12); b1 = _mm_set_epi64x(m3, m7) argument
25 #define LOAD_MSG_2_1(b0, b1) b0 = _mm_set_epi64x(m12, m11); b1 = _mm_set_epi64x(m15, m5) argument
26 #define LOAD_MSG_2_2(b0, b1) b0 = _mm_set_epi64x(m0, m8); b1 = _mm_set_epi64x(m13, m2) argument
[all …]
H A Dblake2b-load-sse41.h17 #define LOAD_MSG_0_1(b0, b1) \ argument
21 b1 = _mm_unpacklo_epi64(m2, m3); \
25 #define LOAD_MSG_0_2(b0, b1) \ argument
29 b1 = _mm_unpackhi_epi64(m2, m3); \
33 #define LOAD_MSG_0_3(b0, b1) \ argument
37 b1 = _mm_unpacklo_epi64(m6, m7); \
41 #define LOAD_MSG_0_4(b0, b1) \ argument
45 b1 = _mm_unpackhi_epi64(m6, m7); \
49 #define LOAD_MSG_1_1(b0, b1) \ argument
53 b1 = _mm_unpackhi_epi64(m4, m6); \
[all …]
H A Dblake2b-round.h47 #define G1(row1l,row2l,row3l,row4l,row1h,row2h,row3h,row4h,b0,b1) \ argument
49 row1h = _mm_add_epi64(_mm_add_epi64(row1h, b1), row2h); \
66 #define G2(row1l,row2l,row3l,row4l,row1h,row2h,row3h,row4h,b0,b1) \ argument
68 row1h = _mm_add_epi64(_mm_add_epi64(row1h, b1), row2h); \
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,b1); \
[all …]
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-load-sse2.h19 #define LOAD_MSG_0_1(b0, b1) \ argument
21 b1 = _mm_set_epi64x(m6, m4)
22 #define LOAD_MSG_0_2(b0, b1) \ argument
24 b1 = _mm_set_epi64x(m7, m5)
25 #define LOAD_MSG_0_3(b0, b1) \ argument
27 b1 = _mm_set_epi64x(m14, m12)
28 #define LOAD_MSG_0_4(b0, b1) \ argument
30 b1 = _mm_set_epi64x(m15, m13)
31 #define LOAD_MSG_1_1(b0, b1) \ argument
33 b1 = _mm_set_epi64x(m13, m9)
[all …]
H A Dblake2b-load-sse41.h19 #define LOAD_MSG_0_1(b0, b1) \ argument
22 b1 = _mm_unpacklo_epi64(m2, m3); \
25 #define LOAD_MSG_0_2(b0, b1) \ argument
28 b1 = _mm_unpackhi_epi64(m2, m3); \
31 #define LOAD_MSG_0_3(b0, b1) \ argument
34 b1 = _mm_unpacklo_epi64(m6, m7); \
37 #define LOAD_MSG_0_4(b0, b1) \ argument
40 b1 = _mm_unpackhi_epi64(m6, m7); \
43 #define LOAD_MSG_1_1(b0, b1) \ argument
46 b1 = _mm_unpackhi_epi64(m4, m6); \
[all …]
H A Dblake2b-compress-sse41.h21 #define G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \ argument
23 row1h = _mm_add_epi64(_mm_add_epi64(row1h, b1), row2h); \
40 #define G2(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \ argument
42 row1h = _mm_add_epi64(_mm_add_epi64(row1h, b1), row2h); \
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, b1); \
[all …]
H A Dblake2b-compress-ssse3.h21 #define G1(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \ argument
23 row1h = _mm_add_epi64(_mm_add_epi64(row1h, b1), row2h); \
40 #define G2(row1l, row2l, row3l, row4l, row1h, row2h, row3h, row4h, b0, b1) \ argument
42 row1h = _mm_add_epi64(_mm_add_epi64(row1h, b1), row2h); \
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, b1); \
[all …]
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-avx2.h12 #define G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
27 ml = _mm256_mul_epu32(A1, B1); \
29 A1 = _mm256_add_epi64(A1, _mm256_add_epi64(B1, ml)); \
37 B1 = _mm256_xor_si256(B1, C1); \
38 B1 = rotr24(B1); \
41 #define G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
55 ml = _mm256_mul_epu32(A1, B1); \
57 A1 = _mm256_add_epi64(A1, _mm256_add_epi64(B1, ml)); \
64 B1 = _mm256_xor_si256(B1, C1); \
65 B1 = rotr63(B1); \
[all …]
H A Dblamka-round-avx512f.h17 #define G1_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
20 A1 = muladd(A1, B1); \
32 B1 = _mm512_xor_si512(B1, C1); \
35 B1 = ror64(B1, 24); \
38 #define G2_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
41 A1 = muladd(A1, B1); \
53 B1 = _mm512_xor_si512(B1, C1); \
56 B1 = ror64(B1, 63); \
59 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
62 B1 = _mm512_permutex_epi64(B1, _MM_SHUFFLE(0, 3, 2, 1)); \
[all …]
H A Dblamka-round-ssse3.h31 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
34 A1 = fBlaMka(A1, B1); \
46 B1 = _mm_xor_si128(B1, C1); \
49 B1 = _mm_roti_epi64(B1, -24); \
52 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
55 A1 = fBlaMka(A1, B1); \
67 B1 = _mm_xor_si128(B1, C1); \
70 B1 = _mm_roti_epi64(B1, -63); \
73 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
75 __m128i t0 = _mm_alignr_epi8(B1, B0, 8); \
[all …]
/freebsd/usr.bin/mididump/
H A Dmididump.c160 uint8_t event, chan, b1, b2; in main() local
190 b1 = read_byte(fd); in main()
192 pn = &notes[b1 % nitems(notes)]; in main()
194 NOTE2OCTAVE(b1)); in main()
197 "/%s%d", pn->alt, NOTE2OCTAVE(b1)); in main()
202 chan, b1, buf, NOTE2FREQ(b1), b2); in main()
205 b1 = read_byte(fd); in main()
209 chan, b1, b2); in main()
212 b1 = read_byte(fd); in main()
214 if (b1 > nitems(ctls) - 1) in main()
[all …]
/freebsd/contrib/gdtoa/
H A DstrtoIg.c41 Bigint *b, *b1; local
54 b1 = Balloc(b->k);
55 Bcopy(b1, b);
63 b1 = increment(b1);
66 b1->x[0] = 0;
67 b1->x[nw1] = 1L << nb11;
76 if (b1->wds > nw
77 || (nb1 && b1->x[nw1] & 1L << nb1)) {
80 rshift(b1, 1);
83 if (b1->x[nw1] & 1L << nb11) {
[all …]
/freebsd/crypto/openssl/crypto/
H A Dc64xpluscpuid.pl35 MVC TSCH,B1
38 MV B1,A5
50 || ZERO B1
53 ||[!B0] CMPLT 1,B4,B1
55 || [B1] STB B2,*B6++[2]
57 ||[!B0] CMPLT 3,B4,B1
59 || [B1] STB B2,*B6++[2]
61 ||[!B0] CMPLT 5,B4,B1
63 || [B1] STB B2,*B6++[2]
76 || [B0] CMPLT 1,B0,B1
[all …]
/freebsd/contrib/libpcap/
H A Dgencode.c927 * Merge the lists in b0 and b1, using the 'sense' field to indicate
931 merge(struct block *b0, struct block *b1) in merge() argument
940 *p = b1; in merge()
1001 gen_and(struct block *b0, struct block *b1) in gen_and() argument
1003 backpatch(b0, b1->head); in gen_and()
1005 b1->sense = !b1->sense; in gen_and()
1006 merge(b1, b0); in gen_and()
1007 b1->sense = !b1->sense; in gen_and()
1008 b1->head = b0->head; in gen_and()
1012 gen_or(struct block *b0, struct block *b1) in gen_or() argument
[all …]
/freebsd/crypto/openssl/fuzz/
H A Dbndiv.c25 static BIGNUM *b1; variable
33 b1 = BN_new(); in FuzzerInitialize()
50 /* s1 and s2 will be the signs for b1 and b2. */ in FuzzerTestOneInput()
57 /* We are going to split the buffer in two, sizes l1 and l2, giving b1 and in FuzzerTestOneInput()
72 OPENSSL_assert(BN_bin2bn(buf, l1, b1) == b1); in FuzzerTestOneInput()
73 BN_set_negative(b1, s1); in FuzzerTestOneInput()
83 OPENSSL_assert(BN_div(b3, b4, b1, b2, ctx)); in FuzzerTestOneInput()
84 if (BN_is_zero(b1)) in FuzzerTestOneInput()
86 else if (BN_is_negative(b1)) in FuzzerTestOneInput()
95 success = success && BN_cmp(b5, b1) == 0; in FuzzerTestOneInput()
[all …]
H A Dbignum.c36 BIGNUM *b1; in FuzzerTestOneInput() local
42 b1 = BN_new(); in FuzzerTestOneInput()
50 * bytes to choose lengths, which generate b1, b2 and b3. Use three bits in FuzzerTestOneInput()
66 OPENSSL_assert(BN_bin2bn(buf, l1, b1) == b1); in FuzzerTestOneInput()
67 BN_set_negative(b1, s1); in FuzzerTestOneInput()
78 OPENSSL_assert(BN_mod_exp(b4, b1, b2, b3, ctx)); in FuzzerTestOneInput()
79 OPENSSL_assert(BN_mod_exp_simple(b5, b1, b2, b3, ctx)); in FuzzerTestOneInput()
83 BN_print_fp(stdout, b1); in FuzzerTestOneInput()
97 BN_free(b1); in FuzzerTestOneInput()
/freebsd/crypto/openssl/crypto/chacha/asm/
H A Dchacha-c64xplus.pl121 my ($b0,$b1,$b2,$b3) = (4..7);
127 ADD @X[$b1],@X[$a1],@X[$a1]
150 XOR @X[$c1],@X[$b1],@X[$b1]
155 ROTL @X[$b1],12,@X[$b1]
162 || ADD @Y[$b1],@Y[$a1],@Y[$a1]
167 || ADD @X[$b1],@X[$a1],@X[$a1]
195 || XOR @Y[$c1],@Y[$b1],@Y[$b1]
201 || XOR @X[$c1],@X[$b1],@X[$b1]
209 || ROTL @Y[$b1],12,@Y[$b1]
211 ROTL @X[$b1],7,@X[$b0] ; avoided cross-path stall
[all …]
/freebsd/sys/cddl/boot/zfs/
H A Dfletcher.c32 uint64_t a0, b0, a1, b1; in fletcher_2_native() local
34 for (a0 = b0 = a1 = b1 = 0; ip < ipend; ip += 2) { in fletcher_2_native()
38 b1 += a1; in fletcher_2_native()
41 ZIO_SET_CHECKSUM(zcp, a0, a1, b0, b1); in fletcher_2_native()
50 uint64_t a0, b0, a1, b1; in fletcher_2_byteswap() local
52 for (a0 = b0 = a1 = b1 = 0; ip < ipend; ip += 2) { in fletcher_2_byteswap()
56 b1 += a1; in fletcher_2_byteswap()
59 ZIO_SET_CHECKSUM(zcp, a0, a1, b0, b1); in fletcher_2_byteswap()
/freebsd/lib/libc/arm/string/
H A Dmemcmp.S156 ldrb r0, [ip, #0x00] /* r0 = b1#0 */
158 subs r0, r0, r3 /* r0 = b1#0 - b2#0 */
159 ldreqb r3, [ip, #0x01] /* r3 = b1#1 */
161 subs r0, r3, r2 /* r0 = b1#1 - b2#1 */
163 ldreqb r0, [ip, #0x02] /* r0 = b1#2 */
166 subs r0, r0, r3 /* r0 = b1#2 - b2#2 */
167 ldreqb r3, [ip, #0x03] /* r3 = b1#3 */
169 subs r0, r3, r2 /* r0 = b1#3 - b2#3 */
171 ldreqb r0, [ip, #0x04] /* r0 = b1#4 */
174 subs r0, r0, r3 /* r0 = b1#4 - b2#4 */
[all …]
/freebsd/contrib/bmake/unit-tests/
H A Ddepsrc-wait.mk19 .PHONY: x a b b1
24 b: b1
26 b1:
27 echo b1
38 three-by-three: .WAIT 3a1 3a2 3a3 .WAIT 3b1 3b2 3b3 .WAIT 3c1 3c2 3c3 .WAIT
39 3a1 3a2 3a3 3b1 3b2 3b3 3c1 3c2 3c3:
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dc64xplus-gf2m.pl28 ($rp,$a1,$a0,$b1,$b0)=("A4","B4","A6","B6","A8"); # argument vector
34 $xFF="B1";
131 || MV $b1,$B
134 &mul_1x1_merged("A28","B28",$A,$B); # a0·b0/a1·b1
136 || XOR $b0,$b1,$B
139 &mul_1x1_merged("A31","B31",$A,$B); # a1·b1/(a0+a1)·(b0+b1)
142 || XOR B28,B31,B29 ; a0·b0+a1·b1
144 &mul_1x1_lower("A30","B30"); # (a0+a1)·(b0+b1)
148 || XOR B29,B30,B30 ; (a0+a1)·(b0+b1)-a0·b0-a1·b1
/freebsd/share/examples/sound/
H A Dmidi.c48 unsigned char raw, type, channel, b1, b2; in main() local
62 if (read(fd, &b1, sizeof(b1)) < sizeof(b1)) in main()
70 channel, b1, b2); in main()
74 channel, b1, b2); in main()
78 channel, b1, b2); in main()
/freebsd/contrib/llvm-project/llvm/lib/Target/AArch64/
H A DAArch64SMEInstrInfo.td75 def RDSVLI_XI : sve_int_read_vl_a<0b0, 0b11111, "rdsvl", /*streaming_sve=*/0b1>;
76 def ADDSPL_XXI : sve_int_arith_vl<0b1, "addspl", /*streaming_sve=*/0b1>;
77 def ADDSVL_XXI : sve_int_arith_vl<0b0, "addsvl", /*streaming_sve=*/0b1>;
84 defm ADDVA_MPPZ_S : sme_add_vector_to_tile_u32<0b1, "addva", int_aarch64_sme_addva>;
89 defm ADDVA_MPPZ_D : sme_add_vector_to_tile_u64<0b1, "addva", int_aarch64_sme_addva>;
101 defm FMOPS_MPPZZ_S : sme_outer_product_fp32<0b1, 0b00, ZPR32, "fmops", int_aarch64_sme_mops>;
106 defm FMOPS_MPPZZ_D : sme_outer_product_fp64<0b1, "fmops", int_aarch64_sme_mops>;
238 (MSRpstatePseudo svcr_op:$pstate, 0b1, timm0_31:$condition)>;
244 (MSRpstatesvcrImm1 svcr_op:$pstate, 0b1)>;
458 defm UCLAMP_VG2_2Z2Z : sme2_int_clamp_vector_vg2_multi<"uclamp", 0b1>;
[all …]
/freebsd/sys/contrib/openzfs/tests/zfs-tests/tests/functional/projectquota/
H A Dprojecttree_002_pos.ksh65 log_must mkdir $PRJDIR/b1
72 log_must mkdir $PRJDIR/b1/a2
73 log_must mkdir $PRJDIR/b1/b2
74 log_must touch $PRJDIR/b1/c2
80 log_must mkdir $PRJDIR/b1/a2/a3
91 log_must zfs project -s $PRJDIR/b1/a2
92 log_must eval "zfs project -d $PRJDIR/b1/a2 | grep ' P '"
93 log_must eval "zfs project -d $PRJDIR/b1/a2/a3 | grep ' \- '"
/freebsd/contrib/llvm-project/llvm/lib/Target/ARM/
H A DARMInstrMVE.td300 def MVE_v16u8 : MVEVectorVTInfo<v16i8, v8i16, v16i1, v8i1, 0b00, "u", 0b1>;
301 def MVE_v8u16 : MVEVectorVTInfo<v8i16, v4i32, v8i1, v4i1, 0b01, "u", 0b1>;
302 def MVE_v4u32 : MVEVectorVTInfo<v4i32, v2i64, v4i1, v2i1, 0b10, "u", 0b1>;
303 def MVE_v2u64 : MVEVectorVTInfo<v2i64, ?, v2i1, ?, 0b11, "u", 0b1>;
312 def MVE_v8p16 : MVEVectorVTInfo<v8i16, v4i32, v8i1, v4i1, 0b11, "p", 0b1>;
446 let Inst{8} = 0b1;
562 "$RdaLo, $RdaHi, $sat, $Rm", op5, 0b1, pattern> {
568 def MVE_ASRLr : MVE_ScalarShiftDRegReg<"asrl", 0b1, [(set tGPREven:$RdaLo, tGPROdd:$RdaHi,
584 def MVE_SQRSHRL : MVE_ScalarShiftDRegRegWithSat<"sqrshrl", 0b1>;
585 def MVE_SQSHLL : MVE_ScalarShiftDRegImm<"sqshll", 0b11, 0b1>;
[all...]

12345678910>>...31