| /optee_os/core/drivers/crypto/caam/utils/ |
| H A D | utils_sgt_v1.c | 22 SGT_TRACE("SGT[%d]->ptr_ms = %" PRIx32, idx, sgt->sgt[idx].v1.ptr_ms); in sgt_entry_trace()
23 SGT_TRACE("SGT[%d]->ptr_ls = %" PRIx32, idx, sgt->sgt[idx].v1.ptr_ls); in sgt_entry_trace()
25 sgt->sgt[idx].v1.len_f_e); in sgt_entry_trace()
26 SGT_TRACE("SGT[%d]->offset = %" PRIx32, idx, sgt->sgt[idx].v1.offset); in sgt_entry_trace()
33 len_f_e = caam_read_val32(&sgt->v1.len_f_e); in sgt_entry_offset()
38 caam_write_val32(&sgt->v1.len_f_e, len_f_e); in sgt_entry_offset()
39 caam_write_val32(&sgt->v1.offset, offset); in sgt_entry_offset()
47 caam_write_val32(&sgt->v1.ptr_ls, paddr); in caam_sgt_set_entry()
49 caam_write_val32(&sgt->v1.ptr_ms, paddr >> 32); in caam_sgt_set_entry()
51 caam_write_val32(&sgt->v1.ptr_ms, 0); in caam_sgt_set_entry()
[all …]
|
| /optee_os/core/arch/arm/crypto/ |
| H A D | aes_modes_armv8a_ce_a64.S | 152 encrypt_block2x v0, v1, w3, x2, x6, w7
157 decrypt_block2x v0, v1, w3, x2, x6, w7
164 encrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
169 decrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
198 encrypt_block2x v0, v1, w3, x2, x6, w7
202 decrypt_block2x v0, v1, w3, x2, x6, w7
206 encrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
210 decrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
220 dup v1.4s, w0
222 aese v0.16b, v1.16b
[all …]
|
| H A D | sm3_armv8a_ce_a64.S | 95 rev32 v1.16b, v1.16b
101 qround a, v0, v1, v2, v3, v4
102 qround a, v1, v2, v3, v4, v0
103 qround a, v2, v3, v4, v0, v1
104 qround a, v3, v4, v0, v1, v2
108 qround b, v4, v0, v1, v2, v3
109 qround b, v0, v1, v2, v3, v4
110 qround b, v1, v2, v3, v4, v0
111 qround b, v2, v3, v4, v0, v1
112 qround b, v3, v4, v0, v1, v2
[all …]
|
| H A D | sha3_armv8a_ce_a64.S | 64 eor v1.8b, v1.8b, v26.8b
129 eor3 v26.16b, v1.16b, v6.16b, v11.16b
146 xar v29.2d, v1.2d, v25.2d, (64 - 1)
147 xar v1.2d, v6.2d, v25.2d, (64 - 44)
198 bcax v4.16b, v28.16b, v1.16b, v0.16b
199 bcax v0.16b, v0.16b, v2.16b, v1.16b
200 bcax v1.16b, v1.16b, v27.16b, v2.16b
|
| H A D | sha512_armv8a_ce_a64.S | 131 mov v1.16b, v9.16b
191 add v9.2d, v9.2d, v1.2d
|
| /optee_os/lib/libutils/isoc/arch/arm/ |
| H A D | arm32_aeabi_ldivmod.c | 60 unsigned long long v1; member
68 unsigned long long denominator = asm_ulqr->v1; in __ul_divmod()
74 asm_ulqr->v1 = qr.r; in __ul_divmod()
79 long long v1; member
87 long long denominator = asm_lqr->v1; in __l_divmod()
103 asm_lqr->v1 = qr.r; in __l_divmod()
|
| H A D | setjmp_a32.S | 209 stmea a1!, { v1-v7, fp, ip, lr }
211 stmea a1!, { v1-v7, fp, ip}
272 ldmfd a1!, { v1-v7, fp, ip, lr }
275 ldmfd a1!, { v1-v7, fp, ip }
|
| /optee_os/lib/libutils/isoc/arch/arm/softfloat/source/include/ |
| H A D | primitiveTypes.h | 71 #define INIT_UINTM4( v3, v2, v1, v0 ) { v0, v1, v2, v3 } argument
82 #define INIT_UINTM4( v3, v2, v1, v0 ) { v3, v2, v1, v0 } argument
|
| /optee_os/core/lib/libtomcrypt/src/ciphers/ |
| H A D | tea.c | 90 ulong32 v0, v1, sum = SUM; in tea_ecb_decrypt() local
99 LOAD32H(v1, &ct[4]); in tea_ecb_decrypt()
102 v1 -= ((v0 << 4) + skey->tea.k[2]) ^ (v0 + sum) ^ ((v0 >> 5) + skey->tea.k[3]); in tea_ecb_decrypt()
103 v0 -= ((v1 << 4) + skey->tea.k[0]) ^ (v1 + sum) ^ ((v1 >> 5) + skey->tea.k[1]); in tea_ecb_decrypt()
108 STORE32H(v1, &pt[4]); in tea_ecb_decrypt()
|
| /optee_os/core/lib/libtomcrypt/src/pk/ecc/ |
| H A D | ecc_recover_key.c | 32 void *r, *s, *v, *w, *t1, *t2, *u1, *u2, *v1, *v2, *e, *x, *y, *a_plus3; in ecc_recover_key() local
49 …if ((err = mp_init_multi(&r, &s, &v, &w, &t1, &t2, &u1, &u2, &v1, &v2, &e, &x, &y, &a_plus3, LTC_N… in ecc_recover_key()
197 …if ((err = mp_mulmod(s, w, p, v1)) != CRYPT_OK) … in ecc_recover_key()
224 …if ((err = ltc_mp.ecc_mul2add(mR, v1, mG, v2, mQ, ma, m)) != CRYPT_OK) … in ecc_recover_key()
255 mp_clear_multi(a_plus3, y, x, e, v2, v1, u2, u1, t2, t1, w, v, s, r, LTC_NULL); in ecc_recover_key()
|
| /optee_os/core/arch/arm/dts/ |
| H A D | embedded_dtb_test.dts | 5 /dts-v1/;
|
| H A D | hikey.dts | 6 /dts-v1/;
|
| H A D | stm32mp157c-ev1-scmi.dts | 5 /dts-v1/;
|
| H A D | stm32mp157a-dk1-scmi.dts | 6 /dts-v1/;
|
| H A D | stm32mp157c-dk2-scmi.dts | 6 /dts-v1/;
|
| H A D | stm32mp215f-dk.dts | 6 /dts-v1/;
|
| H A D | stm32mp157c-dhcom-pdk2.dts | 11 /dts-v1/;
|
| H A D | stm32mp157c-ed1-scmi.dts | 5 /dts-v1/;
|
| H A D | stm32mp157a-dhcor-avenger96.dts | 13 /dts-v1/;
|
| H A D | stm32mp157a-dk1.dts | 7 /dts-v1/;
|
| /optee_os/lib/libmbedtls/mbedtls/library/ |
| H A D | bignum_core.c | 334 size_t i, v0, v1; in mbedtls_mpi_core_shift_r() local
338 v1 = count & (biL - 1); in mbedtls_mpi_core_shift_r()
340 if (v0 > limbs || (v0 == limbs && v1 > 0)) { in mbedtls_mpi_core_shift_r()
361 if (v1 > 0) { in mbedtls_mpi_core_shift_r()
363 r1 = X[i - 1] << (biL - v1); in mbedtls_mpi_core_shift_r()
364 X[i - 1] >>= v1; in mbedtls_mpi_core_shift_r()
374 size_t i, v0, v1; in mbedtls_mpi_core_shift_l() local
378 v1 = count & (biL - 1); in mbedtls_mpi_core_shift_l()
396 if (v1 > 0) { in mbedtls_mpi_core_shift_l()
398 r1 = X[i] >> (biL - v1); in mbedtls_mpi_core_shift_l()
[all …]
|
| H A D | common.h | 207 uint8x16_t v1 = vld1q_u8(a + i); in mbedtls_xor() local
209 uint8x16_t x = veorq_u8(v1, v2); in mbedtls_xor()
|
| /optee_os/core/lib/libtomcrypt/src/stream/sosemanuk/ |
| H A D | sosemanuk.c | 654 STORE32L(u ## x1 ^ v1, st->buf + ooff + 4); \ in s_sosemanuk_internal()
672 ulong32 v0, v1, v2, v3; in s_sosemanuk_internal() local
675 STEP(01, 02, 03, 04, 05, 06, 07, 08, 09, 00, v1, u1); in s_sosemanuk_internal()
680 STEP(05, 06, 07, 08, 09, 00, 01, 02, 03, 04, v1, u1); in s_sosemanuk_internal()
685 STEP(09, 00, 01, 02, 03, 04, 05, 06, 07, 08, v1, u1); in s_sosemanuk_internal()
690 STEP(03, 04, 05, 06, 07, 08, 09, 00, 01, 02, v1, u1); in s_sosemanuk_internal()
695 STEP(07, 08, 09, 00, 01, 02, 03, 04, 05, 06, v1, u1); in s_sosemanuk_internal()
|
| /optee_os/core/arch/arm/plat-totalcompute/fdts/ |
| H A D | optee_sp_manifest.dts | 9 /dts-v1/;
|
| /optee_os/core/drivers/crypto/caam/include/ |
| H A D | caam_utils_sgt.h | 50 } v1; member
|