Home
last modified time | relevance | path

Searched full:a1 (Results 1 – 25 of 1042) sorted by relevance

12345678910>>...42

/freebsd/crypto/openssh/regress/unittests/test_helper/
H A Dtest_helper.h57 const char *a1, const char *a2,
61 const char *a1, const char *a2,
64 const char *a1, const char *a2,
67 const char *a1,
70 const char *a1, const char *a2,
73 const char *a1, const char *a2,
76 const char *a1, const char *a2,
79 const char *a1, const char *a2,
82 const char *a1, const char *a2,
85 const char *a1, const char *a2,
[all …]
H A Dtest_helper.c341 test_header(const char *file, int line, const char *a1, const char *a2, in test_header() argument
348 name, pred_name(pred), a1, in test_header()
354 assert_bignum(const char *file, int line, const char *a1, const char *a2, in assert_bignum() argument
360 test_header(file, line, a1, a2, "BIGNUM", pred); in assert_bignum()
361 fprintf(stderr, "%12s = 0x%s\n", a1, BN_bn2hex(aa1)); in assert_bignum()
368 assert_string(const char *file, int line, const char *a1, const char *a2, in assert_string() argument
374 assert_ptr(file, line, a1, "NULL", aa1, NULL, TEST_NE); in assert_string()
379 test_header(file, line, a1, a2, "STRING", pred); in assert_string()
380 fprintf(stderr, "%12s = %s (len %zu)\n", a1, aa1, strlen(aa1)); in assert_string()
403 assert_mem(const char *file, int line, const char *a1, const char *a2, in assert_mem() argument
[all …]
/freebsd/lib/libc/riscv/string/
H A Dmemset.S11 * register a1 - int c
15 andi a1, a1, 0xFF
22 mul a1, a1, t1
34 sb a1, 1(t0)
35 sb a1, 2(t0)
36 sb a1, 3(t0)
37 sb a1, 4(t0)
38 sb a1, 5(t0)
39 sb a1, 6(t0)
40 sb a1, 7(t0)
[all …]
H A Dmemcpy.S11 * a1 - const void* src
18 sub t0, a0, a1
39 lb t3, 6(a1)
41 lb t3, 5(a1)
43 lb t3, 4(a1)
45 lb t3, 3(a1)
47 lb t3, 2(a1)
49 lb t3, 1(a1)
51 lb t3, 0(a1)
55 add a1, a1, t1
[all …]
H A Dstrrchr.S14 * a1 - int c
19 * a1 - temporary
44 andi a1, a1, 0xFF
47 mul a5, a1, t0
51 ld a1, 0(a0) /* a1 -> data = *ptr_align */
52 not a3, a1 /* a3 -> nhz = ~data */
53 xor a2, a1, a5 /* a2 -> iter = data ^ cccccccc */
54 sub a1, a1, t0 /* a1 -> hz = data - REP8_0X01 */
56 and a1, a1, a3 /* hz = hz & nhz */
58 and a1, a1, t1 /* hz = hz & REP8_0X80 */
[all …]
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/
H A Dblamka-round-avx512f.h17 #define G1_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
20 A1 = muladd(A1, B1); \
23 D1 = _mm512_xor_si512(D1, A1); \
38 #define G2_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
41 A1 = muladd(A1, B1); \
44 D1 = _mm512_xor_si512(D1, A1); \
59 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
71 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
83 #define BLAKE2_ROUND(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
85 G1_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1); \
[all …]
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)); \
30 D1 = _mm256_xor_si256(D1, A1); \
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)); \
58 D1 = _mm256_xor_si256(D1, A1); \
68 #define DIAGONALIZE_1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
79 #define DIAGONALIZE_2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
[all …]
H A Dblamka-round-ssse3.h31 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
34 A1 = fBlaMka(A1, B1); \
37 D1 = _mm_xor_si128(D1, A1); \
52 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
55 A1 = fBlaMka(A1, B1); \
58 D1 = _mm_xor_si128(D1, A1); \
73 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
90 #define UNDIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
107 #define BLAKE2_ROUND(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
109 G1(A0, B0, C0, D0, A1, B1, C1, D1); \
[all …]
/freebsd/sys/contrib/openzfs/tests/zfs-tests/tests/functional/projectquota/
H A Dprojecttree_002_pos.ksh65 log_must mkdir $PRJDIR/a1
69 log_must mkdir $PRJDIR/a1/a2
70 log_must mkdir $PRJDIR/a1/b2
71 log_must touch $PRJDIR/a1/c2
77 log_must mkdir $PRJDIR/a1/a2/a3
78 log_must mkdir $PRJDIR/a1/a2/b3
79 log_must touch $PRJDIR/a1/a2/c3
83 log_must touch $PRJDIR/a1/a2/a3/c4
84 log_must touch $PRJDIR/a1/a2/a3/d4
86 log_must zfs project -p $PRJID1 $PRJDIR/a1/c2
[all …]
H A Dprojecttree_003_neg.ksh65 log_must mkdir $PRJDIR/a1
69 log_mustnot zfs project -c -k $PRJDIR/a1
70 log_mustnot zfs project -c -C $PRJDIR/a1
71 log_mustnot zfs project -c -s $PRJDIR/a1
72 log_must zfs project -c -d -r $PRJDIR/a1
73 log_must zfs project -c -r -d $PRJDIR/a1
78 log_mustnot zfs project -C -c $PRJDIR/a1
79 log_mustnot zfs project -C -d $PRJDIR/a1
80 log_mustnot zfs project -C -p 100 $PRJDIR/a1
81 log_mustnot zfs project -C -s $PRJDIR/a1
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/sanitizer_common/
H A Dsanitizer_syscall_linux_riscv64.inc21 // a0 and a1 (http://man7.org/linux/man-pages/man2/syscall.2.html) arguments
53 #define __internal_syscall1(n, a1) (__internal_syscall)(n, (u64)(a1))
58 register u64 a1 asm("a1") = arg2;
61 : "r"(a7), "r"(a1)
65 #define __internal_syscall2(n, a1, a2) \
66 (__internal_syscall)(n, (u64)(a1), (long)(a2))
71 register u64 a1 asm("a1") = arg2;
75 : "r"(a7), "r"(a1), "r"(a2)
79 #define __internal_syscall3(n, a1, a2, a3) \
80 (__internal_syscall)(n, (u64)(a1), (long)(a2), (long)(a3))
[all …]
H A Dsanitizer_syscall_linux_loongarch64.inc50 #define __internal_syscall1(n, a1) (__internal_syscall)(n, (u64)(a1))
55 register u64 a1 asm("$a1") = arg2;
58 : "r"(a7), "r"(a1)
62 #define __internal_syscall2(n, a1, a2) \
63 (__internal_syscall)(n, (u64)(a1), (long)(a2))
68 register u64 a1 asm("$a1") = arg2;
72 : "r"(a7), "r"(a1), "r"(a2)
76 #define __internal_syscall3(n, a1, a2, a3) \
77 (__internal_syscall)(n, (u64)(a1), (long)(a2), (long)(a3))
83 register u64 a1 asm("$a1") = arg2;
[all …]
/freebsd/crypto/openssl/crypto/
H A Dc64xpluscpuid.pl49 || ZERO A1
52 ||[!B0] CMPLT 0,B4,A1
54 [A1] STB A2,*A4++[2]
56 ||[!B0] CMPLT 2,B4,A1
58 [A1] STB A2,*A4++[2]
60 ||[!B0] CMPLT 4,B4,A1
62 [A1] STB A2,*A4++[2]
64 ||[!B0] CMPLT 6,B4,A1
65 [A1] STB A2,*A4++[2]
75 [B0] CMPLT 0,B0,A1
[all …]
/freebsd/contrib/jemalloc/include/jemalloc/internal/
H A Dprof_inlines_a.h
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dbn-c64xplus.asm124 MV B1,A1
126 || STW A1,*ARG0++(8) ; rp[2*i+1]
138 [B0] ZERO A1 ; carry flag
148 ADDU A1,A9:A8,A1:A0
151 || MV A1,RET ; keep carry flag in RET
172 SUBU B7,A7,A1:A0
173 [A2] SUB A1:A0,1,A1:A0
176 || AND 1,A1,A2 ; pass on borrow flag
179 AND 1,A1,RET ; return borrow flag
186 LMBD 1,A4,A1 ; leading zero bits in hi
[all …]
H A Dx86_64-gf2m.pl50 ($a1,$a2,$a4,$a8,$a12,$a48)=map("%r$_",(9..15));
62 mov \$-1,$a1
64 shr \$3,$a1
66 and $a,$a1 # a1=a&0x1fffffffffffffff
69 lea ($a1,$a1),$a2
71 lea (,$a1,4),$a4
90 mov $a1,$a12
92 xor $a2,$a12 # a1^a2
93 mov $a1,8(%rsp) # tab[1]=a1
97 mov $a12,24(%rsp) # tab[3]=a1^a2
[all …]
H A Dsparcv9-gf2m.pl37 ($a1,$a2,$a4,$a8,$a12,$a48)=map("%o$_",(0..5));
93 mov $a,$a1
101 srax $a1,63,$lo ! broadcast 63rd bit
102 and $a48,$a1,$a1 ! (a<<0)&0x1fff...
104 sllx $a1,3,$a8
110 xor $a1,$a2,$a12
111 stx $a1,[$tab+1*8] ! tab[1]=a1
114 stx $a12,[$tab+3*8] ! tab[3]=a1^a2
115 xor $a4,$a1,$a1
119 stx $a1,[$tab+5*8] ! tab[5]=a1^a4
[all …]
H A Dx86-gf2m.pl57 ($a1,$a2,$a4)=("ecx","edx","ebp");
67 &mov ($a1,$a);
69 &and ($a1,0x3fffffff);
75 &mov (&DWP(1*4,"esp"),$a1); # a1
76 &xor ($a1,$a2); # a1^a2
81 &mov (&DWP(3*4,"esp"),$a1); # a1^a2
84 &xor ($a1,$a2); # a1^a4=a1^a2^a2^a4
89 &mov (&DWP(5*4,"esp"),$a1); # a1^a4
90 &xor ($a4,$a1); # a1^a2^a4
95 &mov (&DWP(7*4,"esp"),$a4); # a1^a2^a4
[all …]
/freebsd/crypto/openssl/crypto/ec/asm/
H A Dx25519-ppc64.pl49 my ($bi,$a0,$a1,$a2,$a3,$t0,$t1, $t2,$t3,
77 ld $a1,8($ap)
83 mulld $acc1,$a1,$bi # a[1]*b[0]
84 mulhdu $t1,$a1,$bi
99 mulld $t1,$a1,$bi
107 mulhdu $t1,$a1,$bi
191 ld $a1,8($ap)
196 # | | | | | |a1*a0| |
199 # | | | |a2*a1| | | |
200 # | | |a3*a1| | | | |
[all …]
/freebsd/sys/dev/enic/
H A Dvnic_dev.c373 u64 *a0, u64 *a1, int wait) in vnic_dev_cmd() argument
379 args[1] = *a1; in vnic_dev_cmd()
399 *a1 = args[1]; in vnic_dev_cmd()
432 u64 a0 = CMD_ADD_ADV_FILTER, a1 = 0; in vnic_dev_capable_adv_filters() local
436 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable_adv_filters()
439 return (a1 >= (u32)FILTER_DPDK_1); in vnic_dev_capable_adv_filters()
499 u64 a0 = CMD_NIC_CFG, a1 = 0; in vnic_dev_capable_udp_rss_weak() local
505 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable_udp_rss_weak()
506 if (err == 0 && a0 != 0 && a1 != 0) { in vnic_dev_capable_udp_rss_weak()
508 *weak = !!((a1 >> 32) & CMD_NIC_CFG_CAPF_UDP_WEAK); in vnic_dev_capable_udp_rss_weak()
[all …]
H A Dvnic_devcmd.h86 * (u16)a1=size of the structure
88 * (u16)a1=0 for in:a1 = 0,
91 * Fills in first 128 bytes of vnic_devcmd_fw_info for in:a1 = 0,
92 * first in:a1 bytes for 0 < in:a1 <= 132,
93 * 132 bytes for other values of in:a1.
101 * in: (u16)a0=offset,(u8)a1=size
110 * (u16)a1=sizeof stats area */
145 * out: (u64) a0= 1 if a1 is valid
146 * (u64) a1= (NIC_CFG bits supported) | (flags << 32)
156 * out: (u64) a0= 1 if a1 is valid
[all …]
/freebsd/lib/libc/softfloat/bits64/
H A Dsoftfloat-macros89 Shifts the 128-bit value formed by concatenating `a0' and `a1' right by 64
97 (This routine makes more sense if `a0' and `a1' are considered to form a
98 fixed-point value with binary point between `a0' and `a1'. This fixed-point
107 bits64 a0, bits64 a1, int16 count, bits64 *z0Ptr, bits64 *z1Ptr )
113 z1 = a1;
117 z1 = ( a0<<negCount ) | ( a1 != 0 );
122 z1 = a0 | ( a1 != 0 );
125 z1 = ( ( a0 | a1 ) != 0 );
136 Shifts the 128-bit value formed by concatenating `a0' and `a1' right by the
145 bits64 a0, bits64 a1, int16 count, bits64 *z0Ptr, bits64 *z1Ptr )
[all …]
/freebsd/sys/sys/
H A Dktr.h145 #define KTR_EVENT2(m, egroup, ident, etype, edat, a0, v0, a1, v1) \ argument
146 CTR4(m, KTR_EFMT(egroup, ident, etype) a0 ", " a1, \
148 #define KTR_EVENT3(m, egroup, ident, etype, edat, a0, v0, a1, v1, a2, v2)\ argument
149 CTR5(m,KTR_EFMT(egroup, ident, etype) a0 ", " a1 ", " a2, \
152 a0, v0, a1, v1, a2, v2, a3, v3) \ argument
153 CTR6(m,KTR_EFMT(egroup, ident, etype) a0 ", " a1 ", " a2 ", " a3,\
163 #define KTR_STATE2(m, egroup, ident, state, a0, v0, a1, v1) \ argument
164 KTR_EVENT2(m, egroup, ident, "state:\"%s\"", state, a0, (v0), a1, (v1))
165 #define KTR_STATE3(m, egroup, ident, state, a0, v0, a1, v1, a2, v2) \ argument
167 state, a0, (v0), a1, (v1), a2, (v2))
[all …]
/freebsd/lib/libc/softfloat/bits32/
H A Dsoftfloat-macros61 Shifts the 64-bit value formed by concatenating `a0' and `a1' right by the
70 bits32 a0, bits32 a1, int16 count, bits32 *z0Ptr, bits32 *z1Ptr )
76 z1 = a1;
80 z1 = ( a0<<negCount ) | ( a1>>count );
94 Shifts the 64-bit value formed by concatenating `a0' and `a1' right by the
99 or 1, depending on whether the concatenation of `a0' and `a1' is zero or
106 bits32 a0, bits32 a1, int16 count, bits32 *z0Ptr, bits32 *z1Ptr )
112 z1 = a1;
116 z1 = ( a0<<negCount ) | ( a1>>count ) | ( ( a1<<negCount ) != 0 );
121 z1 = a0 | ( a1 != 0 );
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/tsan/rtl/
H A Dtsan_rtl_loongarch64.S47 la.local $a1, _ZN14__interception11real_setjmpE
48 ld.d $a1, $a1, 0
49 jr $a1
95 la.local $a1, _ZN14__interception12real__setjmpE
96 ld.d $a1, $a1, 0
97 jr $a1
143 la.local $a1, _ZN14__interception14real_sigsetjmpE
144 ld.d $a1, $a1, 0
145 jr $a1
191 la.local $a1, _ZN14__interception16real___sigsetjmpE
[all …]

12345678910>>...42