| /freebsd-src/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-src/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-src/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 …]
|
| 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-src/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-src/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 | 259 new_posted = (posted + 1) % DEVCMD2_RING_SIZE; in vnic_dev_cmd_proxy()
289 dc2c->color = dc2c->color ? 0 : 1; in vnic_dev_cmd_no_proxy()
337 vdev->args[1] = cmd; in vnic_dev_cmd_args()
346 err = (int)vdev->args[1]; in vnic_dev_cmd_args()
353 memcpy(args, &vdev->args[1], nargs * sizeof(args[0])); in vnic_dev_advanced_filters_cap()
378 u64 *a0, u64 *a1, int wait)
383 args[0] = *a0; in vnic_dev_capable_filter_mode()
384 args[1] = *a1; in vnic_dev_capable_filter_mode()
403 *a0 = args[0]; in vnic_dev_capable_filter_mode()
404 *a1 = args[1]; in vnic_dev_capable_filter_mode()
302 vnic_dev_cmd(struct vnic_dev * vdev,enum vnic_devcmd_cmd cmd,u64 * a0,u64 * a1,int wait) vnic_dev_cmd() argument
361 u64 a0 = CMD_ADD_ADV_FILTER, a1 = 0; vnic_dev_capable_adv_filters() local
428 u64 a0 = CMD_NIC_CFG, a1 = 0; vnic_dev_capable_udp_rss_weak() local
443 u64 a0 = (u32)cmd, a1 = 0; vnic_dev_capable() local
455 u64 a0, a1; vnic_dev_spec() local
487 u64 a0 = 0, a1 = 0; vnic_dev_stats_clear() local
495 u64 a0, a1; vnic_dev_stats_dump() local
553 u64 a0 = 0, a1 = 0; vnic_dev_close() local
561 u64 a0 = 0, a1 = 0; vnic_dev_enable_wait() local
572 u64 a0 = 0, a1 = 0; vnic_dev_disable() local
580 u64 a0 = (u32)arg, a1 = 0; vnic_dev_open() local
588 u64 a0 = 0, a1 = 0; vnic_dev_open_done() local
605 u64 a0 = 0, a1 = 0; vnic_dev_get_mac_addr() local
625 u64 a0, a1 = 0; vnic_dev_packet_filter() local
644 u64 a0 = 0, a1 = 0; vnic_dev_add_addr() local
663 u64 a0 = 0, a1 = 0; vnic_dev_del_addr() local
683 u64 a0 = ig_vlan_rewrite_mode, a1 = 0; vnic_dev_set_ig_vlan_rewrite_mode() local
706 u64 a0, a1; vnic_dev_notify_setcmd() local
759 u64 a0, a1; vnic_dev_notify_unsetcmd() local
815 u64 a0 = (u32)arg, a1 = 0; vnic_dev_init() local
963 u64 a0 = overlay; vnic_dev_overlay_offload_ctrl() local
974 u64 a0 = overlay; vnic_dev_overlay_offload_cfg() local
982 u64 a0 = VIC_FEATURE_VXLAN; vnic_dev_capable_vxlan() local
996 u64 a0 = 0; vnic_dev_counter_alloc() local
1008 u64 a0 = idx; vnic_dev_counter_free() local
1019 u64 a0 = idx; vnic_dev_counter_query() local
[all...] |
| /freebsd-src/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-src/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-src/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-src/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-src/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-src/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-src/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-src/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-src/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-src/usr.bin/mkimg/tests/ |
| 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-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-63x255-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 |
21 000002d0 20 22 31 22 0a 64 64 62 2e 67 65 6f 6d 65 74 72 | "1".ddb.geometr|
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 |................|
56 000007a0 a0 06 00 00 b0 06 00 00 c0 06 00 00 d0 06 00 00 |................|
[all …]
|
| H A D | img-1x1-512-mbr.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 …]
|