Home
last modified time | relevance | path

Searched refs:s0 (Results 1 – 24 of 24) sorted by relevance

/optee_os/lib/libutils/isoc/arch/riscv/
H A Dsetjmp_rv.S10 STR s0, REGOFF(0)(a0)
28 STR s0, REGOFF(2)(sp)
31 STR s0, REGOFF(0)(sp)
33 addi s0, sp, 16
37 LDR s0, REGOFF(2)(sp)
40 LDR s0, REGOFF(0)(sp)
55 STR s0, REGOFF(2)(sp)
57 addi s0, sp, REGOFF(4)
62 LDR s0, REGOFF(2)(sp)
70 LDR s0, REGOFF(0)(a0)
/optee_os/core/arch/riscv/kernel/
H A Darch_scall.c28 unsigned long s0 = 0; in save_panic_regs_rv_ta() local
38 res = GET_USER_SCALAR(s0, stack_s0); in save_panic_regs_rv_ta()
40 s0 = 0; in save_panic_regs_rv_ta()
48 .s0 = s0, in save_panic_regs_rv_ta()
H A Dspinlock.S13 STR s0, REGOFF(0)(sp)
15 mv s0, a0
17 mv a0, s0
22 LDR s0, REGOFF(0)(sp)
H A Dthread_optee_abi_rv.S47 mv s0, a0
63 mv a1, s0
91 STR s0, REGOFF(2)(sp)
95 addi s0, sp, REGOFF(8)
152 LDR s0, REGOFF(4)(sp)
153 csrw CSR_XSTATUS, s0
156 LDR s0, REGOFF(2)(sp)
H A Dentry.S68 sw s0, THREAD_CORE_LOCAL_HART_ID(tp)
126 mv s0, a0 /* Save hart ID into s0 */
198 sw s0, THREAD_CORE_LOCAL_HART_ID(t1)
364 LDR s0, 0(sp)
366 STR s0, 0(s1)
401 sw s0, THREAD_CORE_LOCAL_HART_ID(tp)
H A Dasm-defines.c52 DEFINE(THREAD_CTX_REG_S0, offsetof(struct thread_ctx_regs, s0));
75 DEFINE(THREAD_ABT_REG_S0, offsetof(struct thread_abort_regs, s0));
H A Dthread_rv.S680 get_thread_ctx s0, s1
687 store_xregs s0, THREAD_CTX_KERN_SP, REG_SP
699 csrw CSR_XEPC, s0
702 csrw CSR_XSTATUS, s0
705 csrw CSR_XIE, s0
H A Dabort.c34 .fp = ai->regs->s0, in __print_stack_unwind()
106 ai->regs->t2, ai->regs->s0); in __print_abort_info()
H A Dthread_arch.c512 .s0 = 0, in set_ctx_regs()
/optee_os/core/lib/libtomcrypt/src/ciphers/aes/
H A Daes.c269 ulong32 s0, s1, s2, s3, t0, t1, t2, t3; in s_rijndael_ecb_encrypt() local
288 LOAD32H(s0, pt ); s0 ^= rk[0]; in s_rijndael_ecb_encrypt()
298 Te0(LTC_BYTE(s0, 3)) ^ in s_rijndael_ecb_encrypt()
307 Te3(LTC_BYTE(s0, 0)) ^ in s_rijndael_ecb_encrypt()
312 Te2(LTC_BYTE(s0, 1)) ^ in s_rijndael_ecb_encrypt()
317 Te1(LTC_BYTE(s0, 2)) ^ in s_rijndael_ecb_encrypt()
324 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_rijndael_ecb_encrypt()
336 Te0(LTC_BYTE(s0, 3)) ^ in s_rijndael_ecb_encrypt()
345 Te3(LTC_BYTE(s0, 0)) ^ in s_rijndael_ecb_encrypt()
350 Te2(LTC_BYTE(s0, 1)) ^ in s_rijndael_ecb_encrypt()
[all …]
/optee_os/core/arch/arm/crypto/
H A Dsha256_armv8a_ce_a32.S27 .macro add_only, ev, s0 argument
29 .ifnb \s0
34 .ifnb \s0
35 vadd.u32 ta\ev, q\s0, k\ev
39 .macro add_update, ev, s0, s1, s2, s3
40 sha256su0.32 q\s0, q\s1
42 sha256su1.32 q\s0, q\s2, q\s3
H A Dsha256_armv8a_ce_a64.S28 .macro add_only, ev, rc, s0 argument
31 add t1.4s, v\s0\().4s, \rc\().4s
35 .ifnb \s0
36 add t0.4s, v\s0\().4s, \rc\().4s
43 .macro add_update, ev, rc, s0, s1, s2, s3
44 sha256su0 v\s0\().4s, v\s1\().4s
46 sha256su1 v\s0\().4s, v\s2\().4s, v\s3\().4s
H A Dsm3_armv8a_ce_a64.S44 .macro round, ab, s0, t0, t1, i
49 sm3tt2\ab v9.4s, v5.4s, \s0\().4s, \i
52 .macro qround, ab, s0, s1, s2, s3, s4
55 ext v6.16b, \s0\().16b, \s1\().16b, #12
57 sm3partw1 \s4\().4s, \s0\().4s, \s3\().4s
60 eor v10.16b, \s0\().16b, \s1\().16b
62 round \ab, \s0, v11, v12, 0
63 round \ab, \s0, v12, v11, 1
64 round \ab, \s0, v11, v12, 2
65 round \ab, \s0, v12, v11, 3
H A Dsha1_armv8a_ce_a32.S33 .macro add_only, op, ev, rc, s0, dg1
34 .ifnb \s0
35 vadd.u32 tb\ev, q\s0, \rc
45 .macro add_update, op, ev, rc, s0, s1, s2, s3, dg1
46 sha1su0.32 q\s0, q\s1, q\s2
48 sha1su1.32 q\s0, q\s3
H A Dsha1_armv8a_ce_a64.S33 .macro add_only, op, ev, rc, s0, dg1
35 add t1.4s, v\s0\().4s, \rc\().4s
43 .ifnb \s0
44 add t0.4s, v\s0\().4s, \rc\().4s
51 .macro add_update, op, ev, rc, s0, s1, s2, s3, dg1
52 sha1su0 v\s0\().4s, v\s1\().4s, v\s2\().4s
54 sha1su1 v\s0\().4s, v\s3\().4s
H A Dsm4_armv8a_aese_a64.S252 .macro transpose_4x4, s0, s1, s2, s3
253 zip1 TMP0.4s, \s0\().4s, \s1\().4s
255 zip2 TMP2.4s, \s0\().4s, \s1\().4s
257 zip1 \s0\().2d, TMP0.2d, TMP1.2d
263 .macro rotate_clockwise_90, s0, s1, s2, s3
264 zip1 TMP0.4s, \s1\().4s, \s0\().4s
265 zip2 TMP1.4s, \s1\().4s, \s0\().4s
268 zip1 \s0\().2d, TMP2.2d, TMP0.2d
275 .macro round_4x, s0, s1, s2, s3, k
295 eor TMP4.16b, TMP4.16b, \s0\().16b
[all …]
H A Daes_modes_armv8a_ce_a32.S505 vmov r0, s0
/optee_os/core/lib/libtomcrypt/src/mac/pelican/
H A Dpelican.c50 ulong32 s0, s1, s2, s3, t0, t1, t2, t3; in s_four_rounds() local
53 LOAD32H(s0, pelmac->state ); in s_four_rounds()
59 Te0(LTC_BYTE(s0, 3)) ^ in s_four_rounds()
67 Te3(LTC_BYTE(s0, 0)); in s_four_rounds()
71 Te2(LTC_BYTE(s0, 1)) ^ in s_four_rounds()
75 Te1(LTC_BYTE(s0, 2)) ^ in s_four_rounds()
78 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_four_rounds()
80 STORE32H(s0, pelmac->state ); in s_four_rounds()
/optee_os/lib/libutils/ext/arch/riscv/
H A Dmcount_rv.S66 STR s0, REGOFF(2)(sp)
69 STR s0, REGOFF(0)(sp)
72 addi s0, sp, 16
80 LDR s0, REGOFF(2)(sp)
83 LDR s0, REGOFF(0)(sp)
/optee_os/lib/libutee/arch/riscv/
H A Dutee_syscalls_rv.S30 sw s0, 8(sp)
33 sd s0, 0(sp)
/optee_os/core/arch/riscv/include/kernel/
H A Dthread_arch.h75 unsigned long s0; member
139 unsigned long s0; member
/optee_os/lib/libmbedtls/mbedtls/library/
H A Dsha512.c403 uint64x2_t s0 = (uint64x2_t) vld1q_u8(msg + 16 * 0); in mbedtls_internal_sha512_process_many_a64_crypto() local
413 s0 = vreinterpretq_u64_u8(vrev64q_u8(vreinterpretq_u8_u64(s0))); in mbedtls_internal_sha512_process_many_a64_crypto()
424 initial_sum = vaddq_u64(s0, vld1q_u64(&K[0])); in mbedtls_internal_sha512_process_many_a64_crypto()
481 s0 = vsha512su1q_u64(vsha512su0q_u64(s0, s1), s7, vextq_u64(s4, s5, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
482 initial_sum = vaddq_u64(s0, vld1q_u64(&K[t])); in mbedtls_internal_sha512_process_many_a64_crypto()
489 s1 = vsha512su1q_u64(vsha512su0q_u64(s1, s2), s0, vextq_u64(s5, s6, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
505 s3 = vsha512su1q_u64(vsha512su0q_u64(s3, s4), s2, vextq_u64(s7, s0, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
513 s4 = vsha512su1q_u64(vsha512su0q_u64(s4, s5), s3, vextq_u64(s0, s1, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
537 s7 = vsha512su1q_u64(vsha512su0q_u64(s7, s0), s6, vextq_u64(s3, s4, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
H A Dbn_mul.h1050 mbedtls_mpi_uint s0, s1, b0, b1; \
1056 s0 = ( *s << biH ) >> biH; \
1058 rx = s0 * b1; r0 = s0 * b0; \
/optee_os/core/kernel/
H A Dldelf_loader.c284 arg->rv.fp = tsd->abort_regs.s0; in ldelf_dump_state()