Home
last modified time | relevance | path

Searched refs:reg0 (Results 1 - 25 of 173) sorted by relevance

1234567

/kernel/linux/linux-6.6/arch/s390/include/asm/
H A Dap.h73 unsigned long reg0 = AP_MKQID(0, 0); in ap_instructions_available() local
77 " lgr 0,%[reg0]\n" /* qid into gr0 */ in ap_instructions_available()
85 : [reg0] "d" (reg0) in ap_instructions_available()
177 unsigned long reg0 = qid | (1UL << 24); /* fc 1UL is RAPQ */ in ap_rapq() local
181 reg0 |= 1UL << 22; in ap_rapq()
184 " lgr 0,%[reg0]\n" /* qid arg into gr0 */ in ap_rapq()
188 : [reg0] "d" (reg0) in ap_rapq()
202 unsigned long reg0 in ap_zapq() local
246 unsigned long reg0 = 4UL << 24; /* fc 4UL is QCI */ ap_qci() local
299 unsigned long reg0 = qid | (3UL << 24); /* fc 3UL is AQIC */ ap_aqic() local
347 unsigned long reg0 = qid | (5UL << 24) | ((ifbit & 0x01) << 22); ap_qact() local
377 unsigned long reg0 = qid | (7UL << 24); /* fc 7 is BAPQ */ ap_bapq() local
403 unsigned long reg0 = qid | (8UL << 24); /* fc 8 is AAPQ */ ap_aapq() local
435 unsigned long reg0 = qid | 0x40000000UL; /* 0x4... is last msg part */ ap_nqap() local
494 unsigned long reg0 = resgr0 && *resgr0 ? *resgr0 : qid | 0x80000000UL; ap_dqap() local
[all...]
H A Dfacility.h71 unsigned long reg0 = size - 1; in __stfle_asm() local
74 " lgr 0,%[reg0]\n" in __stfle_asm()
76 " lgr %[reg0],0\n" in __stfle_asm()
77 : [reg0] "+&d" (reg0), [list] "+Q" (*stfle_fac_list) in __stfle_asm()
80 return reg0; in __stfle_asm()
/third_party/ffmpeg/libavcodec/loongarch/
H A Dh264_intrapred_lasx.c30 __m256i reg0, reg1, reg2, reg3, reg4; \
48 reg0 = __lasx_xvldx(src0, -stride); \
50 reg0 = __lasx_xvilvl_d(reg1, reg0); \
51 reg0 = __lasx_xvshuf_b(reg0, reg0, shuff); \
52 reg0 = __lasx_xvhsubw_hu_bu(reg0, reg0); \
[all...]
H A Dvp9_intra_lsx.c435 __m128i tmp0, tmp1, tmp2, tmp3, reg0, reg1; in ff_tm_4x4_lsx() local
439 reg0 = __lsx_vreplgr2vr_h(top_left); in ff_tm_4x4_lsx()
447 DUP4_ARG2(__lsx_vssub_hu, dst0, reg0, dst1, reg0, dst2, reg0, dst3, reg0, in ff_tm_4x4_lsx()
467 __m128i reg0, reg1; in ff_tm_8x8_lsx() local
469 reg0 = __lsx_vreplgr2vr_h(top_left); in ff_tm_8x8_lsx()
483 DUP4_ARG2(__lsx_vssub_hu, src0, reg0, src1, reg0, src in ff_tm_8x8_lsx()
517 __m128i reg0, reg1; ff_tm_16x16_lsx() local
600 __m128i tmp0, tmp1, tmp2, tmp3, reg0, reg1, reg2; ff_tm_32x32_lsx() local
[all...]
H A Dvp9_idct_lsx.c68 #define VP9_DOTP_CONST_PAIR(reg0, reg1, cnst0, cnst1, out0, out1) \
76 s1_m = __lsx_vilvl_h(__lsx_vneg_h(reg1), reg0); \
77 s0_m = __lsx_vilvh_h(__lsx_vneg_h(reg1), reg0); \
78 s3_m = __lsx_vilvl_h(reg0, reg1); \
79 s2_m = __lsx_vilvh_h(reg0, reg1); \
376 __m128i reg0, reg2, reg4, reg6, reg8, reg10, reg12, reg14; in vp9_idct16_1d_columns_addblk_lsx() local
383 reg0, reg1, reg2, reg3); in vp9_idct16_1d_columns_addblk_lsx()
412 VP9_DOTP_CONST_PAIR(reg0, reg8, cospi_16_64, cospi_16_64, reg0, reg8); in vp9_idct16_1d_columns_addblk_lsx()
414 LSX_BUTTERFLY_4_H(reg8, reg0, reg in vp9_idct16_1d_columns_addblk_lsx()
502 __m128i reg0, reg2, reg4, reg6, reg8, reg10, reg12, reg14; 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...]
/kernel/linux/linux-5.10/arch/s390/include/asm/
H A Dap.h56 register unsigned long reg0 asm ("0") = AP_MKQID(0, 0); in ap_instructions_available()
66 : "d" (reg0) in ap_instructions_available()
80 register unsigned long reg0 asm ("0") = qid; in ap_tapq()
86 : "d" (reg0) in ap_tapq()
118 register unsigned long reg0 asm ("0") = qid | (1UL << 24); in ap_rapq()
124 : "d" (reg0) in ap_rapq()
137 register unsigned long reg0 asm ("0") = qid | (2UL << 24); in ap_zapq()
143 : "d" (reg0) in ap_zapq()
175 register unsigned long reg0 asm ("0") = 4UL << 24; in ap_qci()
185 : "d" (reg0), " in ap_qci()
[all...]
H A Dfacility.h64 register unsigned long reg0 asm("0") = size - 1; in __stfle_asm()
68 : "+d" (reg0) in __stfle_asm()
71 return reg0; in __stfle_asm()
/kernel/liteos_a/arch/arm/arm/src/include/
H A Dasm.h50 .macro EXC_SP_SET stackBottom, stackSize, reg0, reg1 variable
51 mrc p15, 0, \reg0, c0, c0, 5 variable
52 and \reg0, \reg0, #MPIDR_CPUID_MASK /* get cpu id */ variable
54 mul \reg1, \reg1, \reg0 /* calculate current cpu stack offset */
55 ldr \reg0, =\stackBottom variable
56 sub \reg0, \reg0, \reg1 /* calculate current cpu stack bottom */ variable
57 mov sp, \reg0 /* set sp */
/kernel/linux/linux-6.6/drivers/media/dvb-frontends/
H A Da8293.c29 u8 reg0, reg1; in a8293_set_voltage_slew() local
105 reg0 = idx_to_reg[this_volt_idx+1]; in a8293_set_voltage_slew()
106 reg0 |= A8293_FLAG_ODT; in a8293_set_voltage_slew()
108 ret = i2c_master_send(client, &reg0, 1); in a8293_set_voltage_slew()
111 dev->reg[0] = reg0; in a8293_set_voltage_slew()
116 reg0 = idx_to_reg[new_volt_idx]; in a8293_set_voltage_slew()
117 reg0 |= A8293_FLAG_ODT; in a8293_set_voltage_slew()
118 ret = i2c_master_send(client, &reg0, 1); in a8293_set_voltage_slew()
121 dev->reg[0] = reg0; in a8293_set_voltage_slew()
148 u8 reg0, reg in a8293_set_voltage_noslew() local
[all...]
H A Dves1820.c30 u8 reg0; member
82 u8 reg0, enum fe_spectral_inversion inversion) in ves1820_setup_reg0()
84 reg0 |= state->reg0 & 0x62; in ves1820_setup_reg0()
87 if (!state->config->invert) reg0 |= 0x20; in ves1820_setup_reg0()
88 else reg0 &= ~0x20; in ves1820_setup_reg0()
90 if (!state->config->invert) reg0 &= ~0x20; in ves1820_setup_reg0()
91 else reg0 |= 0x20; in ves1820_setup_reg0()
94 ves1820_writereg(state, 0x00, reg0 & 0xfe); in ves1820_setup_reg0()
95 ves1820_writereg(state, 0x00, reg0 | in ves1820_setup_reg0()
81 ves1820_setup_reg0(struct ves1820_state *state, u8 reg0, enum fe_spectral_inversion inversion) ves1820_setup_reg0() argument
[all...]
H A Dtda10021.c31 u8 reg0; member
119 static int tda10021_setup_reg0(struct tda10021_state *state, u8 reg0, in tda10021_setup_reg0() argument
122 reg0 |= state->reg0 & 0x63; in tda10021_setup_reg0()
125 reg0 &= ~0x20; in tda10021_setup_reg0()
127 reg0 |= 0x20; in tda10021_setup_reg0()
129 _tda10021_writereg (state, 0x00, reg0 & 0xfe); in tda10021_setup_reg0()
130 _tda10021_writereg (state, 0x00, reg0 | 0x01); in tda10021_setup_reg0()
132 state->reg0 = reg0; in tda10021_setup_reg0()
[all...]
H A Dtua6100.c43 u8 reg0[] = { 0x00, 0x00 }; in tua6100_sleep() local
44 struct i2c_msg msg = { .addr = priv->i2c_address, .flags = 0, .buf = reg0, .len = 2 }; in tua6100_sleep()
63 u8 reg0[] = { 0x00, 0x00 }; in tua6100_set_params() local
66 struct i2c_msg msg0 = { .addr = priv->i2c_address, .flags = 0, .buf = reg0, .len = 2 }; in tua6100_set_params()
76 reg0[1] = 0x03; in tua6100_set_params()
78 reg0[1] = 0x07; in tua6100_set_params()
/kernel/linux/linux-6.6/crypto/
H A Daria_generic.c32 u32 reg0, reg1, reg2, reg3; in aria_set_encrypt_key() local
43 reg0 = w0[0] ^ ck[0]; in aria_set_encrypt_key()
48 aria_subst_diff_odd(&reg0, &reg1, &reg2, &reg3); in aria_set_encrypt_key()
67 w1[0] ^= reg0; in aria_set_encrypt_key()
72 reg0 = w1[0]; in aria_set_encrypt_key()
77 reg0 ^= ck[4]; in aria_set_encrypt_key()
82 aria_subst_diff_even(&reg0, &reg1, &reg2, &reg3); in aria_set_encrypt_key()
84 reg0 ^= w0[0]; in aria_set_encrypt_key()
89 w2[0] = reg0; in aria_set_encrypt_key()
94 reg0 in aria_set_encrypt_key()
200 u32 reg0, reg1, reg2, reg3; __aria_crypt() local
[all...]
/kernel/linux/linux-5.10/drivers/media/dvb-frontends/
H A Da8293.c21 u8 reg0, reg1; in a8293_set_voltage() local
28 reg0 = 0x10; in a8293_set_voltage()
32 reg0 = 0x31; in a8293_set_voltage()
36 reg0 = 0x38; in a8293_set_voltage()
42 if (reg0 != dev->reg[0]) { in a8293_set_voltage()
43 ret = i2c_master_send(client, &reg0, 1); in a8293_set_voltage()
46 dev->reg[0] = reg0; in a8293_set_voltage()
H A Dves1820.c30 u8 reg0; member
82 u8 reg0, enum fe_spectral_inversion inversion) in ves1820_setup_reg0()
84 reg0 |= state->reg0 & 0x62; in ves1820_setup_reg0()
87 if (!state->config->invert) reg0 |= 0x20; in ves1820_setup_reg0()
88 else reg0 &= ~0x20; in ves1820_setup_reg0()
90 if (!state->config->invert) reg0 &= ~0x20; in ves1820_setup_reg0()
91 else reg0 |= 0x20; in ves1820_setup_reg0()
94 ves1820_writereg(state, 0x00, reg0 & 0xfe); in ves1820_setup_reg0()
95 ves1820_writereg(state, 0x00, reg0 | in ves1820_setup_reg0()
81 ves1820_setup_reg0(struct ves1820_state *state, u8 reg0, enum fe_spectral_inversion inversion) ves1820_setup_reg0() argument
[all...]
H A Dtda10021.c31 u8 reg0; member
119 static int tda10021_setup_reg0(struct tda10021_state *state, u8 reg0, in tda10021_setup_reg0() argument
122 reg0 |= state->reg0 & 0x63; in tda10021_setup_reg0()
125 reg0 &= ~0x20; in tda10021_setup_reg0()
127 reg0 |= 0x20; in tda10021_setup_reg0()
129 _tda10021_writereg (state, 0x00, reg0 & 0xfe); in tda10021_setup_reg0()
130 _tda10021_writereg (state, 0x00, reg0 | 0x01); in tda10021_setup_reg0()
132 state->reg0 = reg0; in tda10021_setup_reg0()
[all...]
H A Dtua6100.c43 u8 reg0[] = { 0x00, 0x00 }; in tua6100_sleep() local
44 struct i2c_msg msg = { .addr = priv->i2c_address, .flags = 0, .buf = reg0, .len = 2 }; in tua6100_sleep()
63 u8 reg0[] = { 0x00, 0x00 }; in tua6100_set_params() local
66 struct i2c_msg msg0 = { .addr = priv->i2c_address, .flags = 0, .buf = reg0, .len = 2 }; in tua6100_set_params()
76 reg0[1] = 0x03; in tua6100_set_params()
78 reg0[1] = 0x07; in tua6100_set_params()
/kernel/liteos_a/kernel/user/src/
H A Dlos_user_init.c50 register UINT32 reg0 __asm__("r0") = (UINT32)(parm1); in sys_call3()
55 : "=r"(reg0) in sys_call3()
56 : "i"(SYS_CALL_VALUE), "r"(reg7), "r"(reg0), "r"(reg1), "r"(reg2) in sys_call3()
60 return reg0; in sys_call3()
/kernel/liteos_a/testsuites/unittest/process/basic/pthread/
H A Dit_pthread_test.h49 register int reg0 __asm__("r0") = parm1; in Syscall()
51 __asm__ __volatile__("svc 0" : "=r"(reg0) : "r"(reg7), "r"(reg0), "r"(reg1), "r"(reg2), "r"(reg3) : "memory"); in Syscall()
53 return reg0; in Syscall()
/kernel/linux/linux-5.10/arch/s390/lib/
H A Duaccess.c107 register unsigned long reg0 asm("0") = 0x01UL; in copy_from_user_mvcos()
130 : "d" (reg0) : "cc", "memory"); in copy_from_user_mvcos()
182 register unsigned long reg0 asm("0") = 0x010000UL; in copy_to_user_mvcos()
205 : "d" (reg0) : "cc", "memory"); in copy_to_user_mvcos()
257 register unsigned long reg0 asm("0") = 0x010001UL; in copy_in_user_mvcos()
273 : "d" (reg0) : "cc", "memory"); in copy_in_user_mvcos()
321 register unsigned long reg0 asm("0") = 0x010000UL; in clear_user_mvcos()
343 : "a" (empty_zero_page), "d" (reg0) : "cc", "memory"); in clear_user_mvcos()
396 register unsigned long reg0 asm("0") = 0; in strnlen_user_srst()
411 : "d" (reg0) in strnlen_user_srst()
[all...]
/third_party/node/deps/openssl/openssl/crypto/aria/
H A Daria.c474 register uint32_t reg0, reg1, reg2, reg3; in ossl_aria_encrypt() local
489 reg0 = GET_U32_BE(in, 0); 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()
511 reg0 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
489 reg0 = GET_U32_BE(in, 0); 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()
511 reg0 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/liteos_a/testsuites/unittest/process/basic/process/
H A Dit_test_process.h47 register int reg0 __asm__("r0") = parm1; in Syscall()
49 __asm__ __volatile__("svc 0" : "=r"(reg0) : "r"(reg7), "r"(reg0), "r"(reg1), "r"(reg2), "r"(reg3) : "memory"); in Syscall()
51 return reg0; in Syscall()
/third_party/node/deps/v8/src/codegen/arm64/
H A Dreglist-arm64.h28 explicit CPURegList(CPURegister reg0, CPURegisters... regs) in CPURegList() argument
29 : list_(((uint64_t{1} << reg0.code()) | ... | in CPURegList()
31 size_(reg0.SizeInBits()),
32 type_(reg0.type()) {
33 DCHECK(AreSameSizeAndType(reg0, regs...));
/third_party/mesa3d/src/gallium/drivers/r600/sfn/tests/
H A Dsfn_value_test.cpp92 UniformValue reg0(512, 1); in TEST_F()
94 EXPECT_EQ(reg0.sel(), 512); in TEST_F()
95 EXPECT_EQ(reg0.chan(), 1); in TEST_F()
96 EXPECT_EQ(reg0.kcache_bank(), 0); in TEST_F()
97 EXPECT_FALSE(reg0.buf_addr()); in TEST_F()
98 EXPECT_FALSE(reg0.is_virtual()); in TEST_F()

Completed in 13 milliseconds

1234567