| /freebsd/sys/riscv/vmm/ |
| H A D | vmm_switch.S | 14 * 1. Redistributions of source code must retain the above copyright
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)
[all …]
|
| /freebsd/lib/libc/riscv/gen/ |
| H A D | setjmp.S | 16 * 1. Redistributions of source code must retain the above copyright
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)
[all …]
|
| H A D | _setjmp.S | 16 * 1. Redistributions of source code must retain the above copyright
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)
[all …]
|
| /freebsd/sys/riscv/riscv/ |
| H A D | support.S | 16 * 1. Redistributions of source code must retain the above copyright
42 * One of the fu* or su* functions failed, return -1.
48 li a0, -1
57 bgeu a0, a4, fsu_fault_nopcb
61 lr.w a4, 0(a0) /* Load-exclusive the data */
62 bne a4, a1, 1f /* If not equal then exit */
63 sc.w a5, a3, 0(a0) /* Store the new data */
65 1: li a5, 1 /* Normalize failure result */
69 mv a0, a5 /* Success indicator */
78 bgeu a0, a4, fsu_fault_nopcb
[all …]
|
| H A D | copyinout.S | 17 * 1. Redistributions of source code must retain the above copyright
49 li a0, EFAULT
56 * a0 - Source address
72 andi t0, a0, (XLEN_BYTES-1) /* Low bits of src */
73 andi t1, a1, (XLEN_BYTES-1) /* Low bits of dest */
78 1: lb a4, 0(a0) /* Load byte from src */
79 addi a0, a0, 1
81 addi a1, a1, 1
82 addi a2, a2, -1 /* len-- */
83 andi t0, a0, (XLEN_BYTES-1)
[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 …uffle_epi8(x, _mm256_setr_epi8(3, 4, 5, 6, 7, 0, 1, 2, 11, 12, 13, 14, 15, 8, 9, 10, 3, 4, 5, 6, 7…
9 …le_epi8(x, _mm256_setr_epi8(2, 3, 4, 5, 6, 7, 0, 1, 10, 11, 12, 13, 14, 15, 8, 9, 2, 3, 4, 5, 6, 7…
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 …]
|
| /freebsd/sys/contrib/openzfs/module/lua/setjmp/ |
| H A D | setjmp_rv64g.S | 16 * 1. Redistributions of source code must retain the above copyright
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)
[all …]
|
| H A D | setjmp_loongarch64.S | 8 * 1. Redistributions of source code must retain the above copyright
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 | 9 * 1. Redistributions of source code must retain the above copyright
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 …]
|
| /freebsd/sys/dev/enic/ |
| H A D | vnic_devcmd.h | 14 #define _CMD_NMASK ((1 << _CMD_NBITS)-1)
15 #define _CMD_VTYPEMASK ((1 << _CMD_VTYPEBITS)-1)
16 #define _CMD_FLAGSMASK ((1 << _CMD_FLAGSBITS)-1)
17 #define _CMD_DIRMASK ((1 << _CMD_DIRBITS)-1)
28 #define _CMD_DIR_WRITE 1U
36 #define _CMD_FLAGS_NOWAIT 1U
42 #define _CMD_VTYPE_ENET 1U
74 * (u64)a0=paddr to struct vnic_devcmd_fw_info
80 CMD_MCPU_FW_INFO_OLD = _CMDC(_CMD_DIR_WRITE, _CMD_VTYPE_ALL, 1),
85 * (u64)a0=paddr to struct vnic_devcmd_fw_info
[all …]
|
| H A D | vnic_dev.c | 254 new_posted = (posted + 1) % DEVCMD2_RING_SIZE; in _vnic_dev_cmd2()
284 dc2c->color = dc2c->color ? 0 : 1; in _vnic_dev_cmd2()
332 vdev->args[1] = cmd; in vnic_dev_cmd_proxy()
341 err = (int)vdev->args[1]; in vnic_dev_cmd_proxy()
348 memcpy(args, &vdev->args[1], nargs * sizeof(args[0])); in vnic_dev_cmd_proxy()
373 u64 *a0, u64 *a1, int wait) in vnic_dev_cmd() argument
378 args[0] = *a0; in vnic_dev_cmd()
379 args[1] = *a1; in vnic_dev_cmd()
398 *a0 = args[0]; in vnic_dev_cmd()
399 *a1 = args[1]; in vnic_dev_cmd()
[all …]
|
| /freebsd/sys/cddl/dev/dtrace/riscv/ |
| H A D | dtrace_asm.S | 58 csrrci a0, sstatus, (SSTATUS_SIE)
59 andi a0, a0, (SSTATUS_SIE)
67 csrs sstatus, a0
76 lb a0, 0(a0)
87 lh a0, 0(a0)
98 lw a0, 0(a0)
109 ld a0, 0(a0)
121 1:
122 lb a4, 0(a0) /* Load from uaddr */
123 addi a0, a0, 1
[all …]
|
| /freebsd/sys/dev/psci/ |
| H A D | smccc.h | 13 * 1. Redistributions of source code must retain the above copyright
46 #define SMCCC_FAST_CALL 1
49 #define SMCCC_64BIT_CALL 1
52 #define SMCCC_CPU_SERVICE_CALLS 1
60 register_t a0; member
73 SMCCC_FUNC_ID(SMCCC_FAST_CALL, SMCCC_32BIT_CALL, 0, 1)
81 #define SMCCC_RET_NOT_SUPPORTED -1
95 #define arm_smccc_invoke_1(func, a0, res) \ argument
96 func(a0, 0, 0, 0, 0, 0, 0, 0, res)
97 #define arm_smccc_invoke_2(func, a0, a1, res) \ argument
[all …]
|
| /freebsd/crypto/openssl/crypto/ec/asm/ |
| H A D | x25519-ppc64.pl | 35 $0 =~ m/(.*[\/\\])[^\/\\]+$/; $dir=$1;
49 my ($bi,$a0,$a1,$a2,$a3,$t0,$t1, $t2,$t3,
72 std r31,`$FRAME-8*1`($sp)
75 ld $a0,0($ap)
81 mulld $acc0,$a0,$bi # a[0]*b[0]
82 mulhdu $t0,$a0,$bi
83 mulld $acc1,$a1,$bi # a[1]*b[0]
91 my $i=1; $i<4; shift(@acc), $i++) {
92 my $acc4 = $i==1? $zero : @acc[4];
96 addc @acc[1],@acc[1],$t0 # accumulate high parts
[all …]
|
| /freebsd/lib/libc/softfloat/bits64/ |
| H A D | softfloat-macros | 26 (1) they include prominent notice that the work is derivative, and (2) they
37 the result by setting the least significant bit to 1. The value of `count'
39 result will be either 0 or 1, depending on whether `a' is zero or nonzero.
64 the result by setting the least significant bit to 1. The value of `count'
66 result will be either 0 or 1, depending on whether `a' is zero or nonzero.
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;
[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/crypto/openssl/crypto/bn/asm/ |
| H A D | bn-c64xplus.asm | 72 SPKERNEL 2,1 ; leave slot for "return value"
98 SPKERNEL 2,1 ; leave slot for "return value"
126 || STW A1,*ARG0++(8) ; rp[2*i+1]
148 ADDU A1,A9:A8,A1:A0
150 || STW A0,*A3++ ; write result
172 SUBU B7,A7,A1:A0
173 [A2] SUB A1:A0,1,A1:A0
174 SPKERNEL 0,1 ; leave slot for "return borrow flag"
175 || STW A0,*A3++ ; write result
176 || AND 1,A1,A2 ; pass on borrow flag
[all …]
|
| /freebsd/lib/libc/softfloat/bits32/ |
| H A D | softfloat-macros | 25 (1) they include prominent notice that the work is derivative, and (2) they
36 the result by setting the least significant bit to 1. The value of `count'
38 result will be either 0 or 1, depending on whether `a' is zero or nonzero.
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
[all …]
|
| /freebsd/tests/sys/cddl/zfs/tests/acl/nontrivial/ |
| H A D | zfs_acl_chmod_rwacl_001_pos.ksh | 40 # 1. Separatedly verify file and directory was assigned read_acl/write_acl
69 typeset node=$1
75 chgusr_exec $user $LS -vd $node > /dev/null 2>&1
87 typeset node=$1
97 chgusr_exec $user $CHMOD A0+owner@:read_data:allow $node
105 chgusr_exec $user $CHMOD A0- $node
109 if (( after_cnt - before_cnt != 1 )); then
110 return 1
121 typeset node=$1
125 $CHMOD A0+owner@:read_acl/write_acl:$acc $node
[all …]
|
| /freebsd/contrib/llvm-project/compiler-rt/lib/sanitizer_common/ |
| H A D | sanitizer_syscall_linux_loongarch64.inc | 18 // https://lore.kernel.org/loongarch/1f353678-3398-e30b-1c87-6edb278f74db@xen0n.name/T/#m1613bc86c2…
20 // parameters, if present, are placed in a0-a6
22 // the return value is placed in a0
32 register u64 a0 asm("$a0");
34 : "=r"(a0)
37 return a0;
43 register u64 a0 asm("$a0") = arg1;
45 : "+r"(a0)
48 return a0;
54 register u64 a0 asm("$a0") = arg1;
[all …]
|
| /freebsd/contrib/bearssl/src/symcipher/ |
| H A D | poly1305_ctmulq.c | 55 * If the current accumulator is a = a0 + a1*W + a2*W^2 (where W = 2^44)
58 * a*r = (a0*r0)
59 * + (a0*r1 + a1*r0) * W
60 * + (a0*r2 + a1*r1 + a2*r0) * W^2
68 * b0 = a0*r0 + a1*u2 + a2*u1
69 * b1 = a0*r1 + a1*r0 + a2*u2
70 * b2 = a0*r2 + a1*r1 + a2*r0
75 * b0 = a0*r0 + a1*u2 + a2*t1
76 * b1 = a0*r1 + a1*r0 + a2*t2
77 * b2 = a0*r2 + a1*r1 + a2*r0
[all …]
|
| /freebsd/usr.bin/mkimg/tests/ |
| H A D | img-1x1-512-bsd.vmdk.hex | 9 00000210 72 46 69 6c 65 0a 76 65 72 73 69 6f 6e 3d 31 0a |rFile.version=1.|
18 000002a0 64 64 62 2e 61 64 61 70 74 65 72 54 79 70 65 20 |ddb.adapterType |
22 000002e0 6d 65 74 72 79 2e 68 65 61 64 73 20 3d 20 22 31 |metry.heads = "1|
24 00000300 65 63 74 6f 72 73 20 3d 20 22 31 22 0a 00 00 00 |ectors = "1"....|
32 00000620 a0 00 00 00 b0 00 00 00 c0 00 00 00 d0 00 00 00 |................|
36 00000660 a0 01 00 00 b0 01 00 00 c0 01 00 00 d0 01 00 00 |................|
40 000006a0 a0 02 00 00 b0 02 00 00 c0 02 00 00 d0 02 00 00 |................|
44 000006e0 a0 03 00 00 b0 03 00 00 c0 03 00 00 d0 03 00 00 |................|
48 00000720 a0 04 00 00 b0 04 00 00 c0 04 00 00 d0 04 00 00 |................|
52 00000760 a0 05 00 00 b0 05 00 00 c0 05 00 00 d0 05 00 00 |................|
[all …]
|
| H A D | img-1x1-4096-bsd.vmdk.hex | 9 00000210 72 46 69 6c 65 0a 76 65 72 73 69 6f 6e 3d 31 0a |rFile.version=1.|
18 000002a0 64 64 62 2e 61 64 61 70 74 65 72 54 79 70 65 20 |ddb.adapterType |
22 000002e0 6d 65 74 72 79 2e 68 65 61 64 73 20 3d 20 22 31 |metry.heads = "1|
24 00000300 65 63 74 6f 72 73 20 3d 20 22 31 22 0a 00 00 00 |ectors = "1"....|
32 00000620 a0 00 00 00 b0 00 00 00 c0 00 00 00 d0 00 00 00 |................|
36 00000660 a0 01 00 00 b0 01 00 00 c0 01 00 00 d0 01 00 00 |................|
40 000006a0 a0 02 00 00 b0 02 00 00 c0 02 00 00 d0 02 00 00 |................|
44 000006e0 a0 03 00 00 b0 03 00 00 c0 03 00 00 d0 03 00 00 |................|
48 00000720 a0 04 00 00 b0 04 00 00 c0 04 00 00 d0 04 00 00 |................|
52 00000760 a0 05 00 00 b0 05 00 00 c0 05 00 00 d0 05 00 00 |................|
[all …]
|
| H A D | img-1x1-512-ebr.vmdk.hex | 9 00000210 72 46 69 6c 65 0a 76 65 72 73 69 6f 6e 3d 31 0a |rFile.version=1.|
18 000002a0 64 64 62 2e 61 64 61 70 74 65 72 54 79 70 65 20 |ddb.adapterType |
22 000002e0 6d 65 74 72 79 2e 68 65 61 64 73 20 3d 20 22 31 |metry.heads = "1|
24 00000300 65 63 74 6f 72 73 20 3d 20 22 31 22 0a 00 00 00 |ectors = "1"....|
32 00000620 a0 00 00 00 b0 00 00 00 c0 00 00 00 d0 00 00 00 |................|
36 00000660 a0 01 00 00 b0 01 00 00 c0 01 00 00 d0 01 00 00 |................|
40 000006a0 a0 02 00 00 b0 02 00 00 c0 02 00 00 d0 02 00 00 |................|
44 000006e0 a0 03 00 00 b0 03 00 00 c0 03 00 00 d0 03 00 00 |................|
48 00000720 a0 04 00 00 b0 04 00 00 c0 04 00 00 d0 04 00 00 |................|
52 00000760 a0 05 00 00 b0 05 00 00 c0 05 00 00 d0 05 00 00 |................|
[all …]
|