/freebsd/sys/riscv/vmm/ |
H A D | vmm_switch.S | 39 * 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 D | blamka-round-avx512f.h | 17 #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 D | blamka-round-avx2.h | 7 #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 D | blamka-round-ssse3.h | 8 (_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 D | setjmp.S | 40 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.S | 41 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 D | support.S | 48 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 D | copyinout.S | 49 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 D | swtch.S | 56 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 D | x25519-ppc64.pl | 45 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 D | ecp_nistz256-armv8.pl | 49 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 D | ecp_nistz256-ppc64.pl | 46 $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 D | bn-c64xplus.asm | 60 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 D | mips.pl | 42 # 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 D | x86_64-mont5.pl | 66 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 D | ppc-mont.pl | 168 $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 D | setjmp_loongarch64.S | 32 .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 D | setjmp_mips.S | 14 * 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 D | setjmp_rv64g.S | 42 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 D | chacha-c64xplus.pl | 61 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 D | vnic_devcmd.h | 1 /* 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 D | softfloat-macros | 89 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 D | softfloat-macros | 61 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 D | keccak1600-c64x.pl | 30 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 D | sha512-ppc.pl | 94 @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 …]
|