Home
last modified time | relevance | path

Searched refs:v1 (Results 1 – 25 of 2344) sorted by relevance

12345678910>>...94

/kernel/linux/linux-5.10/drivers/staging/rtl8723bs/hal/
DHalHWImg8723B_BB.c274 u32 v1 = Array[i]; in ODM_ReadAndConfig_MP_8723B_AGC_TAB() local
278 if (v1 < 0x40000000) { in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
279 odm_ConfigBB_AGC_8723B(pDM_Odm, v1, bMaskDWord, v2); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
284 u8 cCond = (u8)((v1 & (BIT29|BIT28)) >> 28); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
288 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
289 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
291 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
292 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
294 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
295 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_AGC_TAB()
[all …]
DHalHWImg8723B_MAC.c245 u32 v1 = Array[i]; in ODM_ReadAndConfig_MP_8723B_MAC_REG() local
249 if (v1 < 0x40000000) { in ODM_ReadAndConfig_MP_8723B_MAC_REG()
250 odm_ConfigMAC_8723B(pDM_Odm, v1, (u8)v2); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
255 u8 cCond = (u8)((v1 & (BIT29|BIT28)) >> 28); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
259 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
260 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_MAC_REG()
262 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
263 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
265 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_MAC_REG()
266 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_MAC_REG()
[all …]
DHalHWImg8723B_RF.c276 u32 v1 = Array[i]; in ODM_ReadAndConfig_MP_8723B_RadioA() local
280 if (v1 < 0x40000000) { in ODM_ReadAndConfig_MP_8723B_RadioA()
281 odm_ConfigRF_RadioA_8723B(pDM_Odm, v1, v2); in ODM_ReadAndConfig_MP_8723B_RadioA()
286 u8 cCond = (u8)((v1 & (BIT29|BIT28)) >> 28); in ODM_ReadAndConfig_MP_8723B_RadioA()
290 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
291 } else if (!CheckPositive(pDM_Odm, v1, v2)) { in ODM_ReadAndConfig_MP_8723B_RadioA()
293 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
294 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
296 READ_NEXT_PAIR(v1, v2, i); in ODM_ReadAndConfig_MP_8723B_RadioA()
297 if (!CheckNegative(pDM_Odm, v1, v2)) in ODM_ReadAndConfig_MP_8723B_RadioA()
[all …]
/kernel/linux/linux-5.10/arch/arm64/crypto/
Daes-ce-ccm-core.S23 eor v1.16b, v1.16b, v1.16b
27 ins v1.b[0], w7
28 ext v1.16b, v1.16b, v1.16b, #1 /* rotate in the input bytes */
31 eor v0.16b, v0.16b, v1.16b
58 ld1 {v1.16b}, [x1], #16 /* load next input block */
59 eor v0.16b, v0.16b, v1.16b /* xor with mac */
77 9: ext v1.16b, v1.16b, v1.16b, #1
80 91: eor v0.16b, v0.16b, v1.16b
95 ld1 {v1.16b}, [x1] /* load 1st ctriv */
104 aese v1.16b, v4.16b
[all …]
Daes-ce-core.S14 ld1 {v1.4s}, [x0], #16
18 mov v3.16b, v1.16b
20 0: mov v2.16b, v1.16b
24 2: ld1 {v1.4s}, [x0], #16
29 aese v0.16b, v1.16b
42 ld1 {v1.4s}, [x0], #16
46 mov v3.16b, v1.16b
48 0: mov v2.16b, v1.16b
52 2: ld1 {v1.4s}, [x0], #16
57 aesd v0.16b, v1.16b
[all …]
/kernel/linux/linux-5.10/arch/s390/crypto/
Dcrc32le-vx.S130 VLM %v1,%v4,0,%r3 /* 64-bytes into V1..V4 */
131 VPERM %v1,%v1,%v1,CONST_PERM_LE2BE
136 VX %v1,%v0,%v1 /* V1 ^= CRC */
158 VGFMAG %v1,CONST_R2R1,%v1,%v5
175 VGFMAG %v1,CONST_R4R3,%v1,%v2
176 VGFMAG %v1,CONST_R4R3,%v1,%v3
177 VGFMAG %v1,CONST_R4R3,%v1,%v4
186 VGFMAG %v1,CONST_R4R3,%v1,%v2 /* Fold next data chunk */
217 VGFMG %v1,%v0,%v1
233 VSRLB %v2,%v1,%v9 /* Store remaining bits in V2 */
[all …]
Dcrc32be-vx.S103 VLM %v1,%v4,0,%r3 /* 64-bytes into V1..V4 */
104 VX %v1,%v0,%v1 /* V1 ^= CRC */
123 VGFMAG %v1,CONST_R1R2,%v1,%v5
137 VGFMAG %v1,CONST_R3R4,%v1,%v2
138 VGFMAG %v1,CONST_R3R4,%v1,%v3
139 VGFMAG %v1,CONST_R3R4,%v1,%v4
148 VGFMAG %v1,CONST_R3R4,%v1,%v2 /* Fold next data chunk */
166 VGFMG %v1,CONST_R5,%v1
175 VGFMG %v1,CONST_R6,%v1
196 VUPLLF %v2,%v1
[all …]
/kernel/linux/linux-5.10/arch/powerpc/lib/
Dxor_vmx.c55 DEFINE(v1); in __xor_altivec_2()
60 LOAD(v1); in __xor_altivec_2()
62 XOR(v1, v2); in __xor_altivec_2()
63 STORE(v1); in __xor_altivec_2()
65 v1 += 4; in __xor_altivec_2()
73 DEFINE(v1); in __xor_altivec_3()
79 LOAD(v1); in __xor_altivec_3()
82 XOR(v1, v2); in __xor_altivec_3()
83 XOR(v1, v3); in __xor_altivec_3()
84 STORE(v1); in __xor_altivec_3()
[all …]
/kernel/linux/linux-5.10/include/pcmcia/
Ddevice_id.h24 #define PCMCIA_DEVICE_PROD_ID1(v1, vh1) { \ argument
26 .prod_id = { (v1), NULL, NULL, NULL }, \
39 #define PCMCIA_DEVICE_PROD_ID12(v1, v2, vh1, vh2) { \ argument
42 .prod_id = { (v1), (v2), NULL, NULL }, \
45 #define PCMCIA_DEVICE_PROD_ID13(v1, v3, vh1, vh3) { \ argument
48 .prod_id = { (v1), NULL, (v3), NULL }, \
51 #define PCMCIA_DEVICE_PROD_ID14(v1, v4, vh1, vh4) { \ argument
54 .prod_id = { (v1), NULL, NULL, (v4) }, \
57 #define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \ argument
61 .prod_id = { (v1), (v2), (v3), NULL },\
[all …]
/kernel/linux/linux-5.10/drivers/char/mwave/
Dmwavedd.h79 #define PRINTK_2(f,s,v1) \ argument
81 printk(s,v1); \
84 #define PRINTK_3(f,s,v1,v2) \ argument
86 printk(s,v1,v2); \
89 #define PRINTK_4(f,s,v1,v2,v3) \ argument
91 printk(s,v1,v2,v3); \
94 #define PRINTK_5(f,s,v1,v2,v3,v4) \ argument
96 printk(s,v1,v2,v3,v4); \
99 #define PRINTK_6(f,s,v1,v2,v3,v4,v5) \ argument
101 printk(s,v1,v2,v3,v4,v5); \
[all …]
/kernel/linux/linux-5.10/arch/s390/include/asm/
Dvx-insn.h94 .ifc \vxr,%v1
200 .macro RXB rxb v1 v2=0 v3=0 v4=0
202 .if \v1 & 0x10
224 .macro MRXB m v1 v2=0 v3=0 v4=0
226 RXB rxb, \v1, \v2, \v3, \v4
239 .macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
240 MRXB \m, \v1, \v2, \v3, \v4
248 VX_NUM v1, \vr
249 .word (0xE700 | ((v1&15) << 4))
251 MRXBOPC 0, 0x44, v1
[all …]
/kernel/linux/linux-5.10/include/linux/
Dprandom.h30 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument
31 v0 += v1, v1 = rol64(v1, 13), v2 += v3, v3 = rol64(v3, 16), \
32 v1 ^= v0, v0 = rol64(v0, 32), v3 ^= v2, \
33 v0 += v3, v3 = rol64(v3, 21), v2 += v1, v1 = rol64(v1, 17), \
34 v3 ^= v0, v1 ^= v2, v2 = rol64(v2, 32) \
46 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument
47 v0 += v1, v1 = rol32(v1, 5), v2 += v3, v3 = rol32(v3, 8), \
48 v1 ^= v0, v0 = rol32(v0, 16), v3 ^= v2, \
49 v0 += v3, v3 = rol32(v3, 7), v2 += v1, v1 = rol32(v1, 13), \
50 v3 ^= v0, v1 ^= v2, v2 = rol32(v2, 16) \
/kernel/linux/linux-5.10/tools/testing/selftests/powerpc/math/
Dvmx_asm.S9 # Should be safe from C, only touches r4, r5 and v0,v1,v2
16 vcmpequd. v1,v0,v20
17 vmr v2,v1
21 vcmpequd. v1,v0,v21
22 vand v2,v2,v1
26 vcmpequd. v1,v0,v22
27 vand v2,v2,v1
31 vcmpequd. v1,v0,v23
32 vand v2,v2,v1
36 vcmpequd. v1,v0,v24
[all …]
/kernel/linux/linux-5.10/arch/arm64/lib/
Dxor-neon.c19 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_2() local
25 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_2()
31 vst1q_u64(dp1 + 2, v1); in xor_arm64_neon_2()
47 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
53 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_3()
59 v1 = veorq_u64(v1, vld1q_u64(dp3 + 2)); in xor_arm64_neon_3()
65 vst1q_u64(dp1 + 2, v1); in xor_arm64_neon_3()
83 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
89 v1 = veorq_u64(vld1q_u64(dp1 + 2), vld1q_u64(dp2 + 2)); in xor_arm64_neon_4()
95 v1 = veorq_u64(v1, vld1q_u64(dp3 + 2)); in xor_arm64_neon_4()
[all …]
/kernel/linux/linux-5.10/lib/
Drandom32.c335 unsigned long v1; member
365 unsigned long v0 = s->v0, v1 = s->v1, v2 = s->v2, v3 = s->v3; in siprand_u32() local
369 PRND_SIPROUND(v0, v1, v2, v3); in siprand_u32()
370 PRND_SIPROUND(v0, v1, v2, v3); in siprand_u32()
372 s->v0 = v0; s->v1 = v1; s->v2 = v2; s->v3 = v3; in siprand_u32()
373 return v1 + v3; in siprand_u32()
440 unsigned long v0 = state->v0, v1 = state->v1; in prandom_seed() local
445 PRND_SIPROUND(v0, v1, v2, v3); in prandom_seed()
446 PRND_SIPROUND(v0, v1, v2, v3); in prandom_seed()
448 } while (unlikely(!v0 || !v1 || !v2 || !v3)); in prandom_seed()
[all …]
Datomic64_test.c107 int v1 = 0xdeadbeef; in test_atomic() local
118 TEST(, or, |=, v1); in test_atomic()
119 TEST(, and, &=, v1); in test_atomic()
120 TEST(, xor, ^=, v1); in test_atomic()
121 TEST(, andnot, &= ~, v1); in test_atomic()
133 FETCH_FAMILY_TEST(, fetch_or, |=, v1); in test_atomic()
134 FETCH_FAMILY_TEST(, fetch_and, &=, v1); in test_atomic()
135 FETCH_FAMILY_TEST(, fetch_andnot, &= ~, v1); in test_atomic()
136 FETCH_FAMILY_TEST(, fetch_xor, ^=, v1); in test_atomic()
141 XCHG_FAMILY_TEST(, v0, v1); in test_atomic()
[all …]
Dxxhash.c110 uint32_t v1 = seed + PRIME32_1 + PRIME32_2; in xxh32() local
116 v1 = xxh32_round(v1, get_unaligned_le32(p)); in xxh32()
126 h32 = xxh_rotl32(v1, 1) + xxh_rotl32(v2, 7) + in xxh32()
180 uint64_t v1 = seed + PRIME64_1 + PRIME64_2; in xxh64() local
186 v1 = xxh64_round(v1, get_unaligned_le64(p)); in xxh64()
196 h64 = xxh_rotl64(v1, 1) + xxh_rotl64(v2, 7) + in xxh64()
198 h64 = xxh64_merge_round(h64, v1); in xxh64()
248 state.v1 = seed + PRIME32_1 + PRIME32_2; in xxh32_reset()
262 state.v1 = seed + PRIME64_1 + PRIME64_2; in xxh64_reset()
293 state->v1 = xxh32_round(state->v1, get_unaligned_le32(p32)); in xxh32_update()
[all …]
/kernel/linux/linux-5.10/tools/arch/x86/lib/
Dx86-opcode-map.txt28 # (v1): this opcode only supports 128bit VEX.
349 # Many AVX instructions lack v1 superscript, according to Intel AVX-Prgramming
351 10: vmovups Vps,Wps | vmovupd Vpd,Wpd (66) | vmovss Vx,Hx,Wss (F3),(v1) | vmovsd Vx,Hx,Wsd (F2),(v1)
352 … vmovups Wps,Vps | vmovupd Wpd,Vpd (66) | vmovss Wss,Hx,Vss (F3),(v1) | vmovsd Wsd,Hx,Vsd (F2),(v1)
353 12: vmovlps Vq,Hq,Mq (v1) | vmovhlps Vq,Hq,Uq (v1) | vmovlpd Vq,Hq,Mq (66),(v1) | vmovsldup Vx,Wx (…
354 13: vmovlps Mq,Vq (v1) | vmovlpd Mq,Vq (66),(v1)
357 16: vmovhps Vdq,Hq,Mq (v1) | vmovlhps Vdq,Hq,Uq (v1) | vmovhpd Vdq,Hq,Mq (66),(v1) | vmovshdup Vx,W…
358 17: vmovhps Mq,Vq (v1) | vmovhpd Mq,Vq (66),(v1)
382 …s Vps,Qpi | cvtpi2pd Vpd,Qpi (66) | vcvtsi2ss Vss,Hss,Ey (F3),(v1) | vcvtsi2sd Vsd,Hsd,Ey (F2),(v1)
384 …tps2pi Ppi,Wps | cvttpd2pi Ppi,Wpd (66) | vcvttss2si Gy,Wss (F3),(v1) | vcvttsd2si Gy,Wsd (F2),(v1)
[all …]
/kernel/linux/linux-5.10/arch/x86/lib/
Dx86-opcode-map.txt28 # (v1): this opcode only supports 128bit VEX.
349 # Many AVX instructions lack v1 superscript, according to Intel AVX-Prgramming
351 10: vmovups Vps,Wps | vmovupd Vpd,Wpd (66) | vmovss Vx,Hx,Wss (F3),(v1) | vmovsd Vx,Hx,Wsd (F2),(v1)
352 … vmovups Wps,Vps | vmovupd Wpd,Vpd (66) | vmovss Wss,Hx,Vss (F3),(v1) | vmovsd Wsd,Hx,Vsd (F2),(v1)
353 12: vmovlps Vq,Hq,Mq (v1) | vmovhlps Vq,Hq,Uq (v1) | vmovlpd Vq,Hq,Mq (66),(v1) | vmovsldup Vx,Wx (…
354 13: vmovlps Mq,Vq (v1) | vmovlpd Mq,Vq (66),(v1)
357 16: vmovhps Vdq,Hq,Mq (v1) | vmovlhps Vdq,Hq,Uq (v1) | vmovhpd Vdq,Hq,Mq (66),(v1) | vmovshdup Vx,W…
358 17: vmovhps Mq,Vq (v1) | vmovhpd Mq,Vq (66),(v1)
382 …s Vps,Qpi | cvtpi2pd Vpd,Qpi (66) | vcvtsi2ss Vss,Hss,Ey (F3),(v1) | vcvtsi2sd Vsd,Hsd,Ey (F2),(v1)
384 …tps2pi Ppi,Wps | cvttpd2pi Ppi,Wpd (66) | vcvttss2si Gy,Wss (F3),(v1) | vcvttsd2si Gy,Wsd (F2),(v1)
[all …]
/kernel/linux/linux-5.10/arch/powerpc/boot/dts/fsl/
Dinterlaken-lac-portals.dtsi39 compatible = "fsl,interlaken-lac-portal-v1.0";
44 compatible = "fsl,interlaken-lac-portal-v1.0";
49 compatible = "fsl,interlaken-lac-portal-v1.0";
54 compatible = "fsl,interlaken-lac-portal-v1.0";
59 compatible = "fsl,interlaken-lac-portal-v1.0";
64 compatible = "fsl,interlaken-lac-portal-v1.0";
69 compatible = "fsl,interlaken-lac-portal-v1.0";
74 compatible = "fsl,interlaken-lac-portal-v1.0";
79 compatible = "fsl,interlaken-lac-portal-v1.0";
84 compatible = "fsl,interlaken-lac-portal-v1.0";
[all …]
/kernel/linux/linux-5.10/drivers/video/fbdev/
Datafb_iplan2p8.c113 u32 pval[4], v, v1, mask; in atafb_iplan2p8_copyarea() local
147 v1 = v & mask; in atafb_iplan2p8_copyarea()
148 *dst32++ = pval[0] | (v1 >> 8); in atafb_iplan2p8_copyarea()
149 pval[0] = (v ^ v1) << 8; in atafb_iplan2p8_copyarea()
151 v1 = v & mask; in atafb_iplan2p8_copyarea()
152 *dst32++ = pval[1] | (v1 >> 8); in atafb_iplan2p8_copyarea()
153 pval[1] = (v ^ v1) << 8; in atafb_iplan2p8_copyarea()
155 v1 = v & mask; in atafb_iplan2p8_copyarea()
156 *dst32++ = pval[2] | (v1 >> 8); in atafb_iplan2p8_copyarea()
157 pval[2] = (v ^ v1) << 8; in atafb_iplan2p8_copyarea()
[all …]
/kernel/linux/linux-5.10/drivers/gpu/drm/amd/display/dc/inc/
Dreg_helper.h67 #define REG_SET_2(reg, init_value, f1, v1, f2, v2) \ argument
69 FN(reg, f1), v1,\
72 #define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \ argument
74 FN(reg, f1), v1,\
78 #define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \ argument
80 FN(reg, f1), v1,\
85 #define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument
88 FN(reg, f1), v1,\
94 #define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \ argument
97 FN(reg, f1), v1,\
[all …]
/kernel/linux/linux-5.10/tools/perf/pmu-events/arch/arm64/
Dmapfile.csv15 0x00000000410fd030,v1,arm/cortex-a53,core
16 0x00000000420f1000,v1,arm/cortex-a53,core
17 0x00000000410fd070,v1,arm/cortex-a57-a72,core
18 0x00000000410fd080,v1,arm/cortex-a57-a72,core
19 0x00000000410fd0b0,v1,arm/cortex-a76-n1,core
20 0x00000000410fd0c0,v1,arm/cortex-a76-n1,core
21 0x00000000420f5160,v1,cavium/thunderx2,core
22 0x00000000430f0af0,v1,cavium/thunderx2,core
23 0x00000000480fd010,v1,hisilicon/hip08,core
24 0x00000000500f0000,v1,ampere/emag,core
/kernel/linux/linux-5.10/arch/powerpc/platforms/ps3/
Drepository.c54 u64 v1, u64 v2, const char *func, int line) in _dump_node() argument
61 pr_devel("%s:%d: v1: %016llx\n", func, line, v1); in _dump_node()
113 u64 v1; in read_node() local
122 result = lv1_read_repository_node(lpar_id, n1, n2, n3, n4, &v1, in read_node()
132 dump_node(lpar_id, n1, n2, n3, n4, v1, v2); in read_node()
135 *_v1 = v1; in read_node()
139 if (v1 && !_v1) in read_node()
141 __func__, __LINE__, v1); in read_node()
169 u64 v1 = 0; in ps3_repository_read_bus_type() local
175 &v1, NULL); in ps3_repository_read_bus_type()
[all …]
/kernel/linux/linux-5.10/arch/mips/kernel/
Dr4k-bugs64.c43 void mult_sh_align_mod(long *v1, long *v2, long *w, in mult_sh_align_mod() argument
113 *v1 = lv1; in mult_sh_align_mod()
120 long v1[8], v2[8], w[8]; in check_mult_sh() local
134 mult_sh_align_mod(&v1[0], &v2[0], &w[0], 32, 0); in check_mult_sh()
135 mult_sh_align_mod(&v1[1], &v2[1], &w[1], 32, 1); in check_mult_sh()
136 mult_sh_align_mod(&v1[2], &v2[2], &w[2], 32, 2); in check_mult_sh()
137 mult_sh_align_mod(&v1[3], &v2[3], &w[3], 32, 3); in check_mult_sh()
138 mult_sh_align_mod(&v1[4], &v2[4], &w[4], 32, 4); in check_mult_sh()
139 mult_sh_align_mod(&v1[5], &v2[5], &w[5], 32, 5); in check_mult_sh()
140 mult_sh_align_mod(&v1[6], &v2[6], &w[6], 32, 6); in check_mult_sh()
[all …]

12345678910>>...94