Home
last modified time | relevance | path

Searched +full:3 +full:a0 (Results 1 – 25 of 839) sorted by relevance

12345678910>>...34

/freebsd/sys/riscv/vmm/
H A Dvmm_switch.S39 * a0 == hypctx *
42 sd ra, (HYP_H_RA)(a0)
43 sd sp, (HYP_H_SP)(a0)
44 sd tp, (HYP_H_TP)(a0)
45 sd gp, (HYP_H_GP)(a0)
46 sd s0, (HYP_H_S + 0 * 8)(a0)
47 sd s1, (HYP_H_S + 1 * 8)(a0)
48 sd s2, (HYP_H_S + 2 * 8)(a0)
49 sd s3, (HYP_H_S + 3 * 8)(a0)
50 sd s4, (HYP_H_S + 4 * 8)(a0)
[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
19 A0 = muladd(A0, B0); \
22 D0 = _mm512_xor_si512(D0, A0); \
38 #define G2_AVX512F(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
40 A0 = muladd(A0, B0); \
43 D0 = _mm512_xor_si512(D0, A0); \
59 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
61 B0 = _mm512_permutex_epi64(B0, _MM_SHUFFLE(0, 3, 2, 1)); \
62 B1 = _mm512_permutex_epi64(B1, _MM_SHUFFLE(0, 3, 2, 1)); \
64 C0 = _mm512_permutex_epi64(C0, _MM_SHUFFLE(1, 0, 3, 2)); \
[all …]
H A Dblamka-round-avx2.h7 #define rotr32(x) _mm256_shuffle_epi32(x, _MM_SHUFFLE(2, 3, 0, 1))
8 …otr24(x) _mm256_shuffle_epi8(x, _mm256_setr_epi8(3, 4, 5, 6, 7, 0, 1, 2, 11, 12, 13, 14, 15, 8, 9,…
9 …16(x) _mm256_shuffle_epi8(x, _mm256_setr_epi8(2, 3, 4, 5, 6, 7, 0, 1, 10, 11, 12, 13, 14, 15, 8, 9…
12 #define G1_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
14 __m256i ml = _mm256_mul_epu32(A0, B0); \
16 A0 = _mm256_add_epi64(A0, _mm256_add_epi64(B0, ml)); \
17 D0 = _mm256_xor_si256(D0, A0); \
41 #define G2_AVX2(A0, A1, B0, B1, C0, C1, D0, D1) \ argument
43 __m256i ml = _mm256_mul_epu32(A0, B0); \
45 A0 = _mm256_add_epi64(A0, _mm256_add_epi64(B0, ml)); \
[all …]
H A Dblamka-round-ssse3.h8 (_mm_setr_epi8(2, 3, 4, 5, 6, 7, 0, 1, 10, 11, 12, 13, 14, 15, 8, 9))
10 (_mm_setr_epi8(3, 4, 5, 6, 7, 0, 1, 2, 11, 12, 13, 14, 15, 8, 9, 10))
13 ? _mm_shuffle_epi32((x), _MM_SHUFFLE(2, 3, 0, 1)) \
31 #define G1(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
33 A0 = fBlaMka(A0, B0); \
36 D0 = _mm_xor_si128(D0, A0); \
52 #define G2(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
54 A0 = fBlaMka(A0, B0); \
57 D0 = _mm_xor_si128(D0, A0); \
73 #define DIAGONALIZE(A0, B0, C0, D0, A1, B1, C1, D1) \ argument
[all …]
/freebsd/lib/libc/riscv/gen/
H A Dsetjmp.S40 sd a0, 0(sp)
44 addi a2, a0, (_JB_SIGMASK * 8) /* oset */
46 li a0, 1 /* SIG_BLOCK */
49 ld a0, 0(sp)
55 sd t0, (0 * 8)(a0)
56 sd sp, (1 * 8)(a0)
57 addi a0, a0, (2 * 8)
60 sd s0, (0 * 8)(a0)
61 sd s1, (1 * 8)(a0)
62 sd s2, (2 * 8)(a0)
[all …]
H A D_setjmp.S41 sd t0, (0 * 8)(a0)
42 sd sp, (1 * 8)(a0)
43 addi a0, a0, (2 * 8)
46 sd s0, (0 * 8)(a0)
47 sd s1, (1 * 8)(a0)
48 sd s2, (2 * 8)(a0)
49 sd s3, (3 * 8)(a0)
50 sd s4, (4 * 8)(a0)
51 sd s5, (5 * 8)(a0)
52 sd s6, (6 * 8)(a0)
[all …]
/freebsd/sys/riscv/riscv/
H A Dsupport.S48 li a0, -1
56 li a4, (VM_MAXUSER_ADDRESS-3)
57 bgeu a0, a4, fsu_fault_nopcb
61 lr.w a4, 0(a0) /* Load-exclusive the data */
63 sc.w a5, a3, 0(a0) /* Store the new data */
69 mv a0, a5 /* Success indicator */
78 bgeu a0, a4, fsu_fault_nopcb
82 lr.d a4, 0(a0) /* Load-exclusive the data */
84 sc.d a5, a3, 0(a0) /* Store the new data */
90 mv a0, a5 /* Success indicator */
[all …]
H A Dcopyinout.S49 li a0, EFAULT
56 * a0 - Source address
72 andi t0, a0, (XLEN_BYTES-1) /* Low bits of src */
78 1: lb a4, 0(a0) /* Load byte from src */
79 addi a0, a0, 1
83 andi t0, a0, (XLEN_BYTES-1)
85 j 3f
88 2: ld a4, 0(a0) /* Load word from src */
89 addi a0, a0, XLEN_BYTES
93 3: bgeu a2, t2, 2b /* Again if len >= XLEN_BYTES */
[all …]
H A Dswtch.S56 fsd f3, (PCB_X + 3 * 16)(\p)
105 fld f3, (PCB_X + 3 * 16)(\p)
146 ld a0, TD_PCB(a0)
147 __fpe_state_save a0
210 mv a0, a1
212 mv a0, s0
215 sd a0, PC_CURTHREAD(tp)
217 ld x13, TD_PCB(a0)
228 ld s3, (PCB_S + 3 * 8)(x13)
239 ld t0, TD_FRAME(a0)
[all …]
/freebsd/crypto/openssl/crypto/ec/asm/
H A Dx25519-ppc64.pl45 my ($rp,$ap,$bp) = map("r$_",3..5);
49 my ($bi,$a0,$a1,$a2,$a3,$t0,$t1, $t2,$t3,
70 std r29,`$FRAME-8*3`($sp)
75 ld $a0,0($ap)
81 mulld $acc0,$a0,$bi # a[0]*b[0]
82 mulhdu $t0,$a0,$bi
87 mulld $acc3,$a3,$bi # a[3]*b[0]
97 mulld $t0,$a0,$bi
100 adde @acc[3],@acc[3],$t2
105 mulhdu $t0,$a0,$bi
[all …]
H A Decp_nistz256-armv8.pl49 my ($rp,$ap,$bp,$bi,$a0,$a1,$a2,$a3,$t0,$t1,$t2,$t3,$poly1,$poly3,
131 ldp $a0,$a1,[$ap]
156 ldp $a0,$a1,[$ap]
182 ldp $a0,$a1,[$ap]
205 ldp $a0,$a1,[$ap]
305 mov $a0,$acc0
312 mov $t0,$a0
317 bl __ecp_nistz256_add // ret += a // 2*a+a=3*a
370 // note that __ecp_nistz256_mul_mont expects a[0-3] input pre-loaded
371 // to $a0-$a3 and b[0] - to $bi
[all …]
H A Decp_nistz256-ppc64.pl46 $acc4,$acc5,$a0,$a1,$a2,$a3,$t0,$t1,$t2,$t3) =
47 map("r$_",(3..12,22..31));
121 ld $a0,0($ap)
148 .byte 0,12,4,0,0x80,10,3,0
169 ld $a0,0($ap)
235 .byte 0,12,4,0,0x80,4,3,0
310 .byte 0,12,4,0,0x80,4,3,0
351 bl __ecp_nistz256_add # ret += a // 2*a+a=3*a
397 .byte 0,12,4,0,0x80,4,3,0
437 # note that __ecp_nistz256_mul_mont expects a[0-3] input pre-loaded
[all …]
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dbn-c64xplus.asm60 NOP 3
65 NOP 3
68 NOP 3 ; [2,0] in epilogue
88 NOP 3
115 NOP 3
122 NOP 3 ; [2,0] in epilogue
140 NOP 3
148 ADDU A1,A9:A8,A1:A0
150 || STW A0,*A3++ ; write result
165 NOP 3
[all …]
H A Dmips.pl42 # goes way over 3 times faster!
52 # >3x performance improvement naturally does not apply to 32-bit code
99 ($zero,$at,$v0,$v1)=map("\$$_",(0..3));
100 ($a0,$a1,$a2,$a3,$a4,$a5,$a6,$a7)=map("\$$_",(4..11));
145 move $a0,$v0
159 $REG_S $t2,3*$SZREG($sp)
173 $LD $t1,0($a0)
175 $LD $t3,$BNSZ($a0)
177 $LD $ta1,2*$BNSZ($a0)
188 $ST $t1,0($a0)
[all …]
H A Dx86_64-mont5.pl66 my $ver = $2 + $3/100.0; # 3.1->3.01, 3.10->3.10
169 lea 24-112(%rsp,$num,8),%r10# place the mask after tp[num+3] (+ICache optimization)
188 pcmpeqd %xmm5,%xmm1 # compare to 3,2
204 movdqa %xmm3,`16*($k+3)+112`(%r10)
224 movdqa %xmm3,`16*($k+3)+112`(%r10)
225 pand `16*($k+3)-128`($bp),%xmm3
235 movdqa `16*($k+3)-128`($bp),%xmm3
240 pand `16*($k+3)+112`(%r10),%xmm3
327 movdqa `16*($k+3)-128`($bp),%xmm3
333 pand `16*($k+3)-128`(%rdx),%xmm3
[all …]
H A Dppc-mont.pl168 $PUSH r29,`-3*$SIZE_T`($tj)
345 $POP r29,`-3*$SIZE_T`($tj)
357 my ($a0,$a1,$a2,$a3,
396 mr $a0,$sp
401 $PUSH r14,-$SIZE_T*18($a0)
402 $PUSH r15,-$SIZE_T*17($a0)
403 $PUSH r16,-$SIZE_T*16($a0)
404 $PUSH r17,-$SIZE_T*15($a0)
405 $PUSH r18,-$SIZE_T*14($a0)
406 $PUSH r19,-$SIZE_T*13($a0)
[all …]
/freebsd/sys/contrib/openzfs/module/lua/setjmp/
H A Dsetjmp_loongarch64.S32 .align 3; \
40 st.d $ra, $a0, 0*8
41 st.d $sp, $a0, 1*8
42 st.d $r21, $a0, 2*8
43 st.d $fp, $a0, 3*8
44 st.d $s0, $a0, 4*8
45 st.d $s1, $a0, 5*8
46 st.d $s2, $a0, 6*8
47 st.d $s3, $a0, 7*8
48 st.d $s4, $a0, 8*8
[all …]
H A Dsetjmp_mips.S14 * 3. Neither the name of the University nor the names of its contributors
51 * jmp_buf is in a0. We need to save s0-s8, sp, gp, and ra in it.
55 REG_S sp, 0(a0) /* save registers */
56 REG_S ra, 1*SZREG(a0)
57 REG_S gp, 2*SZREG(a0)
58 REG_S s0, 3*SZREG(a0)
59 REG_S s1, 4*SZREG(a0)
60 REG_S s2, 5*SZREG(a0)
61 REG_S s3, 6*SZREG(a0)
62 REG_S s4, 7*SZREG(a0)
[all …]
H A Dsetjmp_rv64g.S42 sd sp, (0 * 8)(a0)
43 addi a0, a0, (1 * 8)
46 sd s0, (0 * 8)(a0)
47 sd s1, (1 * 8)(a0)
48 sd s2, (2 * 8)(a0)
49 sd s3, (3 * 8)(a0)
50 sd s4, (4 * 8)(a0)
51 sd s5, (5 * 8)(a0)
52 sd s6, (6 * 8)(a0)
53 sd s7, (7 * 8)(a0)
[all …]
/freebsd/crypto/openssl/crypto/chacha/asm/
H A Dchacha-c64xplus.pl61 MV $LEN,A0 ; reassign
62 [!A0] BNOP RA ; no data
63 || [A0] STW FP,*SP--(40+64) ; save frame pointer and alloca(40+64)
64 || [A0] MV SP,FP
65 [A0] STDW B13:B12,*SP[4+8] ; ABI says so
66 || [A0] MV $KEYB,$KEYA
67 || [A0] MV $COUNTERA,$COUNTERB
68 [A0] STDW B11:B10,*SP[3+8]
69 || [A0] STDW A13:A12,*FP[-3]
70 [A0] STDW A11:A10,*FP[-4]
[all …]
/freebsd/sys/dev/enic/
H A Dvnic_devcmd.h1 /* SPDX-License-Identifier: BSD-3-Clause
74 * (u64)a0=paddr to struct vnic_devcmd_fw_info
85 * (u64)a0=paddr to struct vnic_devcmd_fw_info
101 * in: (u16)a0=offset,(u8)a1=size
102 * out: a0=value
107 CMD_STATS_CLEAR = _CMDCNW(_CMD_DIR_NONE, _CMD_VTYPE_ALL, 3),
109 /* stats dump in mem: (u64)a0=paddr to stats area,
113 /* set Rx packet filter: (u32)a0=filters (see CMD_PFILTER_*) */
116 /* set Rx packet filter for all: (u32)a0=filters (see CMD_PFILTER_*) */
122 /* MAC address in (u48)a0 */
[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 )
114 z0 = a0;
117 z1 = ( a0<<negCount ) | ( a1 != 0 );
118 z0 = a0>>count;
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
[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 )
77 z0 = a0;
80 z1 = ( a0<<negCount ) | ( a1>>count );
81 z0 = a0>>count;
84 z1 = ( count < 64 ) ? ( a0>>( count & 31 ) ) : 0;
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 )
113 z0 = a0;
[all …]
/freebsd/crypto/openssl/crypto/sha/asm/
H A Dkeccak1600-c64x.pl30 my @A = map([ $_, ($_+1), ($_+2), ($_+3), ($_+4) ], (5,10,16,21,26));
32 ($A[3][0],$A[4][1]) = ($A[4][1],$A[3][0]);
33 my @C = (0..4,$A[3][0],$A[4][0]);
38 [ 3, 10, 43, 25, 39 ],
67 # +3--->+------+------+<- -7
75 # +7--->+------+------+<- -3
121 || XOR A$A[0][3],A$A[1][3],A$C[3]
122 || XOR B$A[0][3],B$A[1][3],B$C[3]
127 || XOR A$A[2][3],A$C[3],A$C[3]
128 || XOR B$A[2][3],B$C[3],B$C[3]
[all …]
H A Dsha512-ppc.pl94 @sigma0=( 7,18, 3);
108 $ctx="r3"; # zapped by $a0
113 $a0 ="r3";
137 $ROR $a0,$e,$Sigma1[0]
140 xor $a0,$a0,$a1
146 xor $a0,$a0,$a1 ; Sigma1(e)
148 add $h,$h,$a0
150 $ROR $a0,$a,$Sigma0[0]
154 xor $a0,$a0,$a1
158 xor $a0,$a0,$a1 ; Sigma0(a)
[all …]

12345678910>>...34