Home
last modified time | relevance | path

Searched full:a0 (Results 1 – 25 of 1011) sorted by relevance

12345678910>>...41

/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/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/crypto/krb5/src/tests/asn.1/
H A Dreference_encode.out1 …A0 03 02 01 05 A1 10 1B 0E 41 54 48 45 4E 41 2E 4D 49 54 2E 45 44 55 A2 1A 30 18 A0 03 02 01 01 A1…
2 …ator(optionals empty): 62 4F 30 4D A0 03 02 01 05 A1 10 1B 0E 41 54 48 45 4E 41 2E 4D 49 54 2E 45 …
3 …cator(optionals NULL): 62 4F 30 4D A0 03 02 01 05 A1 10 1B 0E 41 54 48 45 4E 41 2E 4D 49 54 2E 45 …
4 …A0 03 02 01 05 A1 10 1B 0E 41 54 48 45 4E 41 2E 4D 49 54 2E 45 44 55 A2 1A 30 18 A0 03 02 01 01 A1…
5 encode_krb5_keyblock: 30 11 A0 03 02 01 01 A1 0A 04 08 31 32 33 34 35 36 37 38
6 …A0 07 03 05 00 FE DC BA 98 A1 13 30 11 A0 03 02 01 01 A1 0A 04 08 31 32 33 34 35 36 37 38 A2 10 1B…
7 …A0 07 03 05 00 FE DC BA 98 A1 13 30 11 A0 03 02 01 01 A1 0A 04 08 31 32 33 34 35 36 37 38 A2 10 1B…
8 …A0 13 30 11 A0 03 02 01 01 A1 0A 04 08 31 32 33 34 35 36 37 38 A1 36 30 34 30 18 A0 03 02 01 FB A1…
9 …A0 13 30 11 A0 03 02 01 01 A1 0A 04 08 31 32 33 34 35 36 37 38 A1 36 30 34 30 18 A0 03 02 01 FB A1…
10 …A0 03 02 01 05 A1 03 02 01 0B A2 26 30 24 30 10 A1 03 02 01 0D A2 09 04 07 70 61 2D 64 61 74 61 30…
[all …]
H A Dkrb5_decode_test.c115 …A0 03 02 01 05 A1 10 1B 0E 41 54 48 45 4E 41 2E 4D 49 54 2E 45 44 55 A2 1A 30 18 A0 03 02 01 01 A1…
120 " A0 03 02 01 05"
123 " A0 03 02 01 01"
128 " A0 03 02 01 01"
133 " A0 03 02 01 01"
138 " A0 03 02 01 01"
141 " A0 03 02 01 01"
148 " A0 03 02 01 05"
151 " A0 03 02 01 01"
156 " A0 03 02 01 01"
[all …]
H A Dpkinit_encode.out2 …de_krb5_pa_pk_as_rep(dhInfo): A0 28 30 26 80 08 6B 72 62 35 64 61 74 61 A1 0A 04 08 6B 72 62 35 64…
4 …A0 35 30 33 A0 05 02 03 01 E2 40 A1 11 18 0F 31 39 39 34 30 36 31 30 30 36 30 33 31 37 5A A2 03 02…
5 encode_krb5_kdc_dh_key_info: 30 25 A0 0B 03 09 00 6B 72 62 35 64 61 74 61 A1 03 02 01 2A A2 11 18 0…
6 encode_krb5_reply_key_pack: 30 26 A0 13 30 11 A0 03 02 01 01 A1 0A 04 08 31 32 33 34 35 36 37 38 A1…
7 …A0 32 04 30 30 2E A0 10 1B 0E 41 54 48 45 4E 41 2E 4D 49 54 2E 45 44 55 A1 1A 30 18 A0 03 02 01 01…
8 encode_krb5_pkinit_supp_pub_info: 30 1D A0 03 02 01 14 A1 0A 04 08 6B 72 62 35 64 61 74 61 A2 0A 04…
/freebsd/sys/riscv/riscv/
H A Dsupport.S48 li a0, -1
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 */
99 bgeu a0, a1, fsu_fault_nopcb
[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)
88 2: ld a4, 0(a0) /* Load word from src */
89 addi a0, a0, XLEN_BYTES
99 4: lb a4, 0(a0) /* Load byte from src */
100 addi a0, a0, 1
[all …]
/freebsd/sys/contrib/openzfs/module/lua/setjmp/
H A Dsetjmp_rv64g.S43 sd sp, (0 * 8)(a0)
44 addi a0, a0, (1 * 8)
47 sd s0, (0 * 8)(a0)
48 sd s1, (1 * 8)(a0)
49 sd s2, (2 * 8)(a0)
50 sd s3, (3 * 8)(a0)
51 sd s4, (4 * 8)(a0)
52 sd s5, (5 * 8)(a0)
53 sd s6, (6 * 8)(a0)
54 sd s7, (7 * 8)(a0)
[all …]
H A Dsetjmp_loongarch64.S41 st.d $ra, $a0, 0*8
42 st.d $sp, $a0, 1*8
43 st.d $r21, $a0, 2*8
44 st.d $fp, $a0, 3*8
45 st.d $s0, $a0, 4*8
46 st.d $s1, $a0, 5*8
47 st.d $s2, $a0, 6*8
48 st.d $s3, $a0, 7*8
49 st.d $s4, $a0, 8*8
50 st.d $s5, $a0, 9*8
[all …]
H A Dsetjmp_mips.S52 * jmp_buf is in a0. We need to save s0-s8, sp, gp, and ra in it.
56 REG_S sp, 0(a0) /* save registers */
57 REG_S ra, 1*SZREG(a0)
58 REG_S gp, 2*SZREG(a0)
59 REG_S s0, 3*SZREG(a0)
60 REG_S s1, 4*SZREG(a0)
61 REG_S s2, 5*SZREG(a0)
62 REG_S s3, 6*SZREG(a0)
63 REG_S s4, 7*SZREG(a0)
64 REG_S s5, 8*SZREG(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
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
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)); \
46 D0 = _mm256_xor_si256(D0, A0); \
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 …]
/freebsd/sys/dev/enic/
H A Dvnic_devcmd.h74 * (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
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 */
127 /* add addr from (u48)a0 */
131 /* del addr from (u48)a0 */
[all …]
H A Dvnic_dev.c373 u64 *a0, u64 *a1, int wait) in vnic_dev_cmd() argument
378 args[0] = *a0; in vnic_dev_cmd()
398 *a0 = args[0]; 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()
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()
514 u64 a0 = (u32)cmd, a1 = 0; in vnic_dev_capable() local
518 err = vnic_dev_cmd(vdev, CMD_CAPABILITY, &a0, &a1, wait); in vnic_dev_capable()
[all …]
/freebsd/sys/cddl/dev/dtrace/riscv/
H A Ddtrace_asm.S58 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)
122 lb a4, 0(a0) /* Load from uaddr */
123 addi a0, a0, 1
143 lb a4, 0(a0) /* Load from uaddr */
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/sanitizer_common/
H A Dsanitizer_syscall_linux_loongarch64.inc20 // 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;
57 : "+r"(a0)
[all …]
H A Dsanitizer_syscall_linux_riscv64.inc21 // a0 and a1 (http://man7.org/linux/man-pages/man2/syscall.2.html) arguments
22 // are passed in: a0-a7 (see below)
35 register u64 a0 asm("a0");
37 : "=r"(a0)
40 return a0;
46 register u64 a0 asm("a0") = arg1;
48 : "+r"(a0)
51 return a0;
57 register u64 a0 asm("a0") = arg1;
60 : "+r"(a0)
[all …]
H A Dsanitizer_common_interceptors_vfork_loongarch64.inc.S22 // store $ra by $a0
23 st.d $ra, $a0, 0
27 la.local $a0, _ZN14__interception10real_vforkE
28 ld.d $a0, $a0, 0
29 jirl $ra, $a0, 0
33 // store $a0 by adjusted stack
34 st.d $a0, $sp, 8
35 // jump to exit label if $a0 is 0
36 beqz $a0, .L_exit
38 // $a0 != 0 => parent process. Clear stack shadow.
[all …]
/freebsd/sys/dev/psci/
H A Dsmccc.h60 register_t a0; member
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
98 func(a0, a1, 0, 0, 0, 0, 0, 0, res)
99 #define arm_smccc_invoke_3(func, a0, a1, a2, res) \ argument
100 func(a0, a1, a2, 0, 0, 0, 0, 0, res)
101 #define arm_smccc_invoke_4(func, a0, a1, a2, a3, res) \ argument
102 func(a0, a1, a2, a3, 0, 0, 0, 0, res)
103 #define arm_smccc_invoke_5(func, a0, a1, a2, a3, a4, res) \ argument
[all …]
/freebsd/sys/sys/
H A Dktr.h143 #define KTR_EVENT1(m, egroup, ident, etype, edat, a0, v0) \ argument
144 CTR3(m, KTR_EFMT(egroup, ident, etype) a0, ident, edat, (v0))
145 #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,\
161 #define KTR_STATE1(m, egroup, ident, state, a0, v0) \ argument
162 KTR_EVENT1(m, egroup, ident, "state:\"%s\"", state, a0, (v0))
[all …]
/freebsd/crypto/openssl/crypto/ec/asm/
H A Dx25519-ppc64.pl49 my ($bi,$a0,$a1,$a2,$a3,$t0,$t1, $t2,$t3,
75 ld $a0,0($ap)
81 mulld $acc0,$a0,$bi # a[0]*b[0]
82 mulhdu $t0,$a0,$bi
97 mulld $t0,$a0,$bi
105 mulhdu $t0,$a0,$bi
189 ld $a0,0($ap)
196 # | | | | | |a1*a0| |
197 # | | | | |a2*a0| | |
198 # | |a3*a2|a3*a0| | | |
[all …]
/freebsd/contrib/jemalloc/include/jemalloc/internal/
H A Dprof_inlines_a.h12 uint64_t a0, a1; in prof_accum_add() local
21 a0 = atomic_load_u64(&prof_accum->accumbytes, ATOMIC_RELAXED); in prof_accum_add()
23 a1 = a0 + accumbytes; in prof_accum_add()
24 assert(a1 >= a0); in prof_accum_add()
29 } while (!atomic_compare_exchange_weak_u64(&prof_accum->accumbytes, &a0, in prof_accum_add()
33 a0 = prof_accum->accumbytes; in prof_accum_add()
34 a1 = a0 + accumbytes; in prof_accum_add()
56 uint64_t a0, a1; in prof_accum_cancel() local
58 a0 = atomic_load_u64(&prof_accum->accumbytes, ATOMIC_RELAXED); in prof_accum_cancel()
60 a1 = (a0 >= SC_LARGE_MINCLASS - usize) in prof_accum_cancel()
[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/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 …]

12345678910>>...41