Home
last modified time | relevance | path

Searched refs:reg3 (Results 1 - 25 of 113) sorted by relevance

12345

/kernel/linux/linux-6.6/crypto/
H A Daria_generic.c32 u32 reg0, reg1, reg2, reg3; in aria_set_encrypt_key() local
46 reg3 = w0[3] ^ ck[3]; in aria_set_encrypt_key()
48 aria_subst_diff_odd(&reg0, &reg1, &reg2, &reg3); in aria_set_encrypt_key()
70 w1[3] ^= reg3; in aria_set_encrypt_key()
75 reg3 = w1[3]; in aria_set_encrypt_key()
80 reg3 ^= ck[7]; in aria_set_encrypt_key()
82 aria_subst_diff_even(&reg0, &reg1, &reg2, &reg3); in aria_set_encrypt_key()
87 reg3 ^= w0[3]; in aria_set_encrypt_key()
92 w2[3] = reg3; in aria_set_encrypt_key()
97 reg3 in aria_set_encrypt_key()
200 u32 reg0, reg1, reg2, reg3; __aria_crypt() local
[all...]
/kernel/linux/linux-6.6/arch/arm/lib/
H A Dcopy_from_user.S46 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
49 ldr1w \ptr, \reg3, \abort
53 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
54 ldr4w \ptr, \reg1, \reg2, \reg3, \reg4, \abort
66 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
67 USERL(\abort, ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4})
70 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
71 USERL(\abort, ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8})
86 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
87 stmia \ptr!, {\reg1, \reg2, \reg3, \reg
[all...]
H A Dcopy_to_user.S40 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
41 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4}
44 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
45 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8}
64 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
67 str1w \ptr, \reg3, \abort
83 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
84 USERL(\abort, stmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8})
H A Dmemcpy.S21 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
22 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4}
25 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
26 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8}
37 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
38 stmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8}
/kernel/linux/linux-5.10/arch/arm/lib/
H A Dcopy_from_user.S46 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
49 ldr1w \ptr, \reg3, \abort
53 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
54 ldr4w \ptr, \reg1, \reg2, \reg3, \reg4, \abort
66 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
67 USERL(\abort, ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4})
70 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
71 USERL(\abort, ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8})
86 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
87 stmia \ptr!, {\reg1, \reg2, \reg3, \reg
[all...]
H A Dmemcpy.S21 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
22 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4}
25 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
26 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8}
37 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
38 stmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8}
H A Dcopy_to_user.S40 .macro ldr4w ptr reg1 reg2 reg3 reg4 abort
41 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4}
44 .macro ldr8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
45 ldmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8}
64 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
67 str1w \ptr, \reg3, \abort
83 .macro str8w ptr reg1 reg2 reg3 reg4 reg5 reg6 reg7 reg8 abort
84 USERL(\abort, stmia \ptr!, {\reg1, \reg2, \reg3, \reg4, \reg5, \reg6, \reg7, \reg8})
/kernel/linux/linux-5.10/arch/arm/probes/kprobes/
H A Dtest-core.h246 #define TEST_RRR(code1, reg1, val1, code2, reg2, val2, code3, reg3, val3, code4)\
247 TESTCASE_START(code1 #reg1 code2 #reg2 code3 #reg3 code4) \
250 TEST_ARG_REG(reg3, val3) \
252 TEST_INSTRUCTION(code1 #reg1 code2 #reg2 code3 #reg3 code4) \
255 #define TEST_RRRR(code1, reg1, val1, code2, reg2, val2, code3, reg3, val3, code4, reg4, val4) \
256 TESTCASE_START(code1 #reg1 code2 #reg2 code3 #reg3 code4 #reg4) \
259 TEST_ARG_REG(reg3, val3) \
262 TEST_INSTRUCTION(code1 #reg1 code2 #reg2 code3 #reg3 code4 #reg4) \
288 #define TEST_PRR(code1, reg1, val1, code2, reg2, val2, code3, reg3, val3, code4)\
289 TESTCASE_START(code1 #reg1 code2 #reg2 code3 #reg3 code
[all...]
/kernel/linux/linux-6.6/arch/arm/probes/kprobes/
H A Dtest-core.h247 #define TEST_RRR(code1, reg1, val1, code2, reg2, val2, code3, reg3, val3, code4)\
248 TESTCASE_START(code1 #reg1 code2 #reg2 code3 #reg3 code4) \
251 TEST_ARG_REG(reg3, val3) \
253 TEST_INSTRUCTION(code1 #reg1 code2 #reg2 code3 #reg3 code4) \
256 #define TEST_RRRR(code1, reg1, val1, code2, reg2, val2, code3, reg3, val3, code4, reg4, val4) \
257 TESTCASE_START(code1 #reg1 code2 #reg2 code3 #reg3 code4 #reg4) \
260 TEST_ARG_REG(reg3, val3) \
263 TEST_INSTRUCTION(code1 #reg1 code2 #reg2 code3 #reg3 code4 #reg4) \
289 #define TEST_PRR(code1, reg1, val1, code2, reg2, val2, code3, reg3, val3, code4)\
290 TESTCASE_START(code1 #reg1 code2 #reg2 code3 #reg3 code
[all...]
/kernel/linux/linux-5.10/arch/arm64/include/asm/
H A Dkvm_ptrauth.h69 .macro ptrauth_switch_to_guest g_ctxt, reg1, reg2, reg3
77 ptrauth_restore_state \reg1, \reg2, \reg3
81 .macro ptrauth_switch_to_hyp g_ctxt, h_ctxt, reg1, reg2, reg3
89 ptrauth_save_state \reg1, \reg2, \reg3
91 ptrauth_restore_state \reg1, \reg2, \reg3
97 .macro ptrauth_switch_to_guest g_ctxt, reg1, reg2, reg3
99 .macro ptrauth_switch_to_hyp g_ctxt, h_ctxt, reg1, reg2, reg3
/kernel/linux/linux-6.6/arch/arm64/include/asm/
H A Dkvm_ptrauth.h69 .macro ptrauth_switch_to_guest g_ctxt, reg1, reg2, reg3
77 ptrauth_restore_state \reg1, \reg2, \reg3
81 .macro ptrauth_switch_to_hyp g_ctxt, h_ctxt, reg1, reg2, reg3
89 ptrauth_save_state \reg1, \reg2, \reg3
91 ptrauth_restore_state \reg1, \reg2, \reg3
97 .macro ptrauth_switch_to_guest g_ctxt, reg1, reg2, reg3
99 .macro ptrauth_switch_to_hyp g_ctxt, h_ctxt, reg1, reg2, reg3
/third_party/ffmpeg/libavcodec/loongarch/
H A Dvp9_idct_lsx.c377 __m128i reg1, reg3, reg5, reg7, reg9, reg11, reg13, reg15; in vp9_idct16_1d_columns_addblk_lsx() local
383 reg0, reg1, reg2, reg3); in vp9_idct16_1d_columns_addblk_lsx()
435 VP9_DOTP_CONST_PAIR(reg13, reg3, cospi_6_64, cospi_26_64, loc0, loc1); in vp9_idct16_1d_columns_addblk_lsx()
436 LSX_BUTTERFLY_4_H(loc0, loc1, reg11, reg5, reg13, reg3, reg11, reg5); in vp9_idct16_1d_columns_addblk_lsx()
438 loc1 = __lsx_vadd_h(reg15, reg3); in vp9_idct16_1d_columns_addblk_lsx()
439 reg3 = __lsx_vsub_h(reg15, reg3); in vp9_idct16_1d_columns_addblk_lsx()
472 VP9_DOTP_CONST_PAIR(reg3, reg13, cospi_16_64, cospi_16_64, reg3, reg13); in vp9_idct16_1d_columns_addblk_lsx()
473 LSX_BUTTERFLY_4_H(reg12, reg14, reg13, reg3, reg in vp9_idct16_1d_columns_addblk_lsx()
501 __m128i reg1, reg3, reg5, reg7, reg9, reg11, reg13, reg15; vp9_idct16_1d_columns_lsx() local
883 __m128i reg0, reg1, reg2, reg3, reg4, reg5, reg6, reg7; vp9_idct8x32_column_even_process_store() local
998 __m128i reg0, reg1, reg2, reg3, reg4, reg5, reg6, reg7; vp9_idct8x32_column_odd_process_store() local
[all...]
H A Dh264_intrapred_lasx.c30 __m256i reg0, reg1, reg2, reg3, reg4; \
74 reg3 = __lasx_xvmul_w(reg0, int_mult1); \
76 reg4 = __lasx_xvadd_w(reg4, reg3); \
78 tmp0 = __lasx_xvadd_w(reg2, reg3); \
83 tmp2 = __lasx_xvadd_w(reg2, reg3); \
/third_party/node/deps/openssl/openssl/crypto/aria/
H A Daria.c474 register uint32_t reg0, reg1, reg2, reg3; in ossl_aria_encrypt() local
492 reg3 = GET_U32_BE(in, 3); in ossl_aria_encrypt()
494 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
497 ARIA_SUBST_DIFF_ODD(reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
498 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
502 ARIA_SUBST_DIFF_EVEN(reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
503 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
506 ARIA_SUBST_DIFF_ODD(reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
507 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
526 reg3 in ossl_aria_encrypt()
541 register uint32_t reg0, reg1, reg2, reg3; ossl_aria_set_encrypt_key() local
676 register uint32_t reg0, reg1, reg2, reg3; ossl_aria_set_decrypt_key() local
[all...]
/third_party/openssl/crypto/aria/
H A Daria.c474 register uint32_t reg0, reg1, reg2, reg3; in ossl_aria_encrypt() local
492 reg3 = GET_U32_BE(in, 3); in ossl_aria_encrypt()
494 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
497 ARIA_SUBST_DIFF_ODD(reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
498 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
502 ARIA_SUBST_DIFF_EVEN(reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
503 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
506 ARIA_SUBST_DIFF_ODD(reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
507 ARIA_ADD_ROUND_KEY(rk, reg0, reg1, reg2, reg3); in ossl_aria_encrypt()
526 reg3 in ossl_aria_encrypt()
541 register uint32_t reg0, reg1, reg2, reg3; ossl_aria_set_encrypt_key() local
676 register uint32_t reg0, reg1, reg2, reg3; ossl_aria_set_decrypt_key() local
[all...]
/kernel/linux/linux-5.10/arch/s390/kernel/
H A Dcpcmd.c30 register unsigned long reg3 asm ("3") = cmdlen; in diag8_noresponse()
34 : "+d" (reg3) : "d" (reg2) : "cc"); in diag8_noresponse()
35 return reg3; in diag8_noresponse()
43 register unsigned long reg3 asm ("3") = (addr_t) response; in diag8_response()
53 : "d" (reg2), "d" (reg3), "d" (*rlen) : "cc"); in diag8_response()
/kernel/linux/linux-5.10/arch/s390/kvm/
H A Dtrace.h287 TP_PROTO(VCPU_PROTO_COMMON, int g, int reg1, int reg3, u64 addr),
288 TP_ARGS(VCPU_ARGS_COMMON, g, reg1, reg3, addr),
294 __field(int, reg3)
302 __entry->reg3 = reg3;
308 __entry->reg1, __entry->reg3, __entry->addr)
312 TP_PROTO(VCPU_PROTO_COMMON, int g, int reg1, int reg3, u64 addr),
313 TP_ARGS(VCPU_ARGS_COMMON, g, reg1, reg3, addr),
319 __field(int, reg3)
327 __entry->reg3
[all...]
/kernel/linux/linux-6.6/arch/s390/kvm/
H A Dtrace.h287 TP_PROTO(VCPU_PROTO_COMMON, int g, int reg1, int reg3, u64 addr),
288 TP_ARGS(VCPU_ARGS_COMMON, g, reg1, reg3, addr),
294 __field(int, reg3)
302 __entry->reg3 = reg3;
308 __entry->reg1, __entry->reg3, __entry->addr)
312 TP_PROTO(VCPU_PROTO_COMMON, int g, int reg1, int reg3, u64 addr),
313 TP_ARGS(VCPU_ARGS_COMMON, g, reg1, reg3, addr),
319 __field(int, reg3)
327 __entry->reg3
[all...]
/third_party/vixl/src/aarch64/
H A Dregisters-aarch64.h975 const CPURegister& reg3 = NoReg,
989 const CPURegister regs[] = {reg1, reg2, reg3, reg4, reg5, reg6, reg7, reg8};
1031 const CPURegister& reg3 = NoCPUReg,
1040 match &= !reg3.IsValid() || reg3.IsSameSizeAndType(reg1);
1055 const CPURegister& reg3 = NoReg,
1064 even &= !reg3.IsValid() || ((reg3.GetCode() % 2) == 0);
1080 const CPURegister& reg3 = NoCPUReg,
1091 if (!reg3
[all...]
/kernel/linux/linux-5.10/sound/soc/codecs/
H A Drt715-sdw.c151 unsigned int reg2 = 0, reg3 = 0, reg4 = 0, mask, nid, val2; in rt715_sdw_read() local
173 reg3 = RT715_PRIV_DATA_R_H | nid; in rt715_sdw_read()
174 ret = regmap_write(rt715->sdw_regmap, reg3, in rt715_sdw_read()
178 reg4 = reg3 + 0x1000; in rt715_sdw_read()
261 reg, reg2, reg3, reg4, *val); in rt715_sdw_read()
273 unsigned int reg2 = 0, reg3, reg4, nid, mask, val2; in rt715_sdw_write() local
295 reg3 = RT715_PRIV_DATA_W_H | nid; in rt715_sdw_write()
296 ret = regmap_write(rt715->sdw_regmap, reg3, in rt715_sdw_write()
300 reg4 = reg3 + 0x1000; in rt715_sdw_write()
340 __func__, reg, reg2, reg3, reg in rt715_sdw_write()
[all...]
H A Drt711-sdw.c93 unsigned int reg2 = 0, reg3 = 0, reg4 = 0, mask, nid, val2; in rt711_sdw_read() local
115 reg3 = RT711_PRIV_DATA_R_H | nid; in rt711_sdw_read()
117 reg3, ((*val >> 8) & 0xff)); in rt711_sdw_read()
120 reg4 = reg3 + 0x1000; in rt711_sdw_read()
203 __func__, reg, reg2, reg3, reg4, *val); in rt711_sdw_read()
215 unsigned int reg2 = 0, reg3, reg4, nid, mask, val2; in rt711_sdw_write() local
237 reg3 = RT711_PRIV_DATA_W_H | nid; in rt711_sdw_write()
239 reg3, ((val >> 8) & 0xff)); in rt711_sdw_write()
242 reg4 = reg3 + 0x1000; in rt711_sdw_write()
282 __func__, reg, reg2, reg3, reg in rt711_sdw_write()
[all...]
H A Drt700-sdw.c89 unsigned int reg2 = 0, reg3 = 0, reg4 = 0, mask, nid, val2; in rt700_sdw_read() local
111 reg3 = RT700_PRIV_DATA_R_H | nid; in rt700_sdw_read()
113 reg3, ((*val >> 8) & 0xff)); in rt700_sdw_read()
116 reg4 = reg3 + 0x1000; in rt700_sdw_read()
199 __func__, reg, reg2, reg3, reg4, *val); in rt700_sdw_read()
211 unsigned int reg2 = 0, reg3, reg4, nid, mask, val2; in rt700_sdw_write() local
233 reg3 = RT700_PRIV_DATA_W_H | nid; in rt700_sdw_write()
235 reg3, ((val >> 8) & 0xff)); in rt700_sdw_write()
238 reg4 = reg3 + 0x1000; in rt700_sdw_write()
278 __func__, reg, reg2, reg3, reg in rt700_sdw_write()
[all...]
/kernel/linux/linux-6.6/sound/soc/codecs/
H A Drt715-sdw.c152 unsigned int reg2 = 0, reg3 = 0, reg4 = 0, mask, nid, val2; in rt715_sdw_read() local
174 reg3 = RT715_PRIV_DATA_R_H | nid; in rt715_sdw_read()
175 ret = regmap_write(rt715->sdw_regmap, reg3, in rt715_sdw_read()
179 reg4 = reg3 + 0x1000; in rt715_sdw_read()
262 reg, reg2, reg3, reg4, *val); in rt715_sdw_read()
274 unsigned int reg2 = 0, reg3, reg4, nid, mask, val2; in rt715_sdw_write() local
296 reg3 = RT715_PRIV_DATA_W_H | nid; in rt715_sdw_write()
297 ret = regmap_write(rt715->sdw_regmap, reg3, in rt715_sdw_write()
301 reg4 = reg3 + 0x1000; in rt715_sdw_write()
341 __func__, reg, reg2, reg3, reg in rt715_sdw_write()
[all...]
H A Drt700-sdw.c90 unsigned int reg2 = 0, reg3 = 0, reg4 = 0, mask, nid, val2; in rt700_sdw_read() local
112 reg3 = RT700_PRIV_DATA_R_H | nid; in rt700_sdw_read()
114 reg3, ((*val >> 8) & 0xff)); in rt700_sdw_read()
117 reg4 = reg3 + 0x1000; in rt700_sdw_read()
200 __func__, reg, reg2, reg3, reg4, *val); in rt700_sdw_read()
212 unsigned int reg2 = 0, reg3, reg4, nid, mask, val2; in rt700_sdw_write() local
234 reg3 = RT700_PRIV_DATA_W_H | nid; in rt700_sdw_write()
236 reg3, ((val >> 8) & 0xff)); in rt700_sdw_write()
239 reg4 = reg3 + 0x1000; in rt700_sdw_write()
279 __func__, reg, reg2, reg3, reg in rt700_sdw_write()
[all...]
H A Drt711-sdw.c94 unsigned int reg2 = 0, reg3 = 0, reg4 = 0, mask, nid, val2; in rt711_sdw_read() local
116 reg3 = RT711_PRIV_DATA_R_H | nid; in rt711_sdw_read()
118 reg3, ((*val >> 8) & 0xff)); in rt711_sdw_read()
121 reg4 = reg3 + 0x1000; in rt711_sdw_read()
204 __func__, reg, reg2, reg3, reg4, *val); in rt711_sdw_read()
216 unsigned int reg2 = 0, reg3, reg4, nid, mask, val2; in rt711_sdw_write() local
238 reg3 = RT711_PRIV_DATA_W_H | nid; in rt711_sdw_write()
240 reg3, ((val >> 8) & 0xff)); in rt711_sdw_write()
243 reg4 = reg3 + 0x1000; in rt711_sdw_write()
283 __func__, reg, reg2, reg3, reg in rt711_sdw_write()
[all...]

Completed in 12 milliseconds

12345