Symbol: v3
arch/arm64/kvm/vgic/vgic-debug.c
148
bool v3 = dist->vgic_model == KVM_DEV_TYPE_ARM_VGIC_V3;
arch/arm64/kvm/vgic/vgic-debug.c
153
seq_printf(s, "vgic_model:\t%s\n", v3 ? "GICv3" : "GICv2");
arch/arm64/kvm/vgic/vgic-debug.c
155
if (v3)
arch/arm64/lib/xor-neon.c
100
v3 = veorq_u64(v3, vld1q_u64(dp3 + 6));
arch/arm64/lib/xor-neon.c
106
v3 = veorq_u64(v3, vld1q_u64(dp4 + 6));
arch/arm64/lib/xor-neon.c
112
vst1q_u64(dp1 + 6, v3);
arch/arm64/lib/xor-neon.c
133
register uint64x2_t v0, v1, v2, v3;
arch/arm64/lib/xor-neon.c
141
v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6));
arch/arm64/lib/xor-neon.c
147
v3 = veorq_u64(v3, vld1q_u64(dp3 + 6));
arch/arm64/lib/xor-neon.c
153
v3 = veorq_u64(v3, vld1q_u64(dp4 + 6));
arch/arm64/lib/xor-neon.c
159
v3 = veorq_u64(v3, vld1q_u64(dp5 + 6));
arch/arm64/lib/xor-neon.c
165
vst1q_u64(dp1 + 6, v3);
arch/arm64/lib/xor-neon.c
19
register uint64x2_t v0, v1, v2, v3;
arch/arm64/lib/xor-neon.c
203
register uint64x2_t v0, v1, v2, v3;
arch/arm64/lib/xor-neon.c
214
v3 = eor3(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6),
arch/arm64/lib/xor-neon.c
221
vst1q_u64(dp1 + 6, v3);
arch/arm64/lib/xor-neon.c
240
register uint64x2_t v0, v1, v2, v3;
arch/arm64/lib/xor-neon.c
251
v3 = eor3(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6),
arch/arm64/lib/xor-neon.c
258
v3 = veorq_u64(v3, vld1q_u64(dp4 + 6));
arch/arm64/lib/xor-neon.c
264
vst1q_u64(dp1 + 6, v3);
arch/arm64/lib/xor-neon.c
27
v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6));
arch/arm64/lib/xor-neon.c
286
register uint64x2_t v0, v1, v2, v3;
arch/arm64/lib/xor-neon.c
297
v3 = eor3(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6),
arch/arm64/lib/xor-neon.c
304
v3 = eor3(v3, vld1q_u64(dp4 + 6), vld1q_u64(dp5 + 6));
arch/arm64/lib/xor-neon.c
310
vst1q_u64(dp1 + 6, v3);
arch/arm64/lib/xor-neon.c
33
vst1q_u64(dp1 + 6, v3);
arch/arm64/lib/xor-neon.c
48
register uint64x2_t v0, v1, v2, v3;
arch/arm64/lib/xor-neon.c
56
v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6));
arch/arm64/lib/xor-neon.c
62
v3 = veorq_u64(v3, vld1q_u64(dp3 + 6));
arch/arm64/lib/xor-neon.c
68
vst1q_u64(dp1 + 6, v3);
arch/arm64/lib/xor-neon.c
86
register uint64x2_t v0, v1, v2, v3;
arch/arm64/lib/xor-neon.c
94
v3 = veorq_u64(vld1q_u64(dp1 + 6), vld1q_u64(dp2 + 6));
arch/loongarch/lib/xor_template.c
100
: : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3), [v4] "r"(v4),
arch/loongarch/lib/xor_template.c
106
v3 += LINE_WIDTH / sizeof(unsigned long);
arch/loongarch/lib/xor_template.c
38
const unsigned long * __restrict v3)
arch/loongarch/lib/xor_template.c
46
LD_AND_XOR_LINE(v3)
arch/loongarch/lib/xor_template.c
48
: : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3) : "memory"
arch/loongarch/lib/xor_template.c
53
v3 += LINE_WIDTH / sizeof(unsigned long);
arch/loongarch/lib/xor_template.c
60
const unsigned long * __restrict v3,
arch/loongarch/lib/xor_template.c
69
LD_AND_XOR_LINE(v3)
arch/loongarch/lib/xor_template.c
72
: : [v1] "r"(v1), [v2] "r"(v2), [v3] "r"(v3), [v4] "r"(v4)
arch/loongarch/lib/xor_template.c
78
v3 += LINE_WIDTH / sizeof(unsigned long);
arch/loongarch/lib/xor_template.c
86
const unsigned long * __restrict v3,
arch/loongarch/lib/xor_template.c
96
LD_AND_XOR_LINE(v3)
arch/powerpc/lib/xor_vmx.c
103
DEFINE(v3);
arch/powerpc/lib/xor_vmx.c
110
LOAD(v3);
arch/powerpc/lib/xor_vmx.c
113
XOR(v3, v4);
arch/powerpc/lib/xor_vmx.c
114
XOR(v1, v3);
arch/powerpc/lib/xor_vmx.c
119
v3 += 4;
arch/powerpc/lib/xor_vmx.c
133
DEFINE(v3);
arch/powerpc/lib/xor_vmx.c
141
LOAD(v3);
arch/powerpc/lib/xor_vmx.c
145
XOR(v3, v4);
arch/powerpc/lib/xor_vmx.c
147
XOR(v1, v3);
arch/powerpc/lib/xor_vmx.c
152
v3 += 4;
arch/powerpc/lib/xor_vmx.c
78
DEFINE(v3);
arch/powerpc/lib/xor_vmx.c
84
LOAD(v3);
arch/powerpc/lib/xor_vmx.c
86
XOR(v1, v3);
arch/powerpc/lib/xor_vmx.c
91
v3 += 4;
arch/s390/include/asm/fpu-insn-asm.h
103
.ifc \vxr,%v3
arch/s390/include/asm/fpu-insn-asm.h
219
.macro RXB rxb v1 v2=0 v3=0 v4=0
arch/s390/include/asm/fpu-insn-asm.h
246
.macro MRXB m v1 v2=0 v3=0 v4=0
arch/s390/include/asm/fpu-insn-asm.h
264
.macro MRXBOPC m opc v1 v2=0 v3=0 v4=0
arch/s390/include/asm/fpu-insn-asm.h
372
VX_NUM v3, \vr
arch/s390/include/asm/fpu-insn-asm.h
373
.word 0xE700 | (r1 << 4) | (v3&15)
arch/s390/include/asm/fpu-insn-asm.h
375
MRXBOPC \m, 0x21, 0, v3
arch/s390/include/asm/fpu-insn-asm.h
393
VX_NUM v3, \vto
arch/s390/include/asm/fpu-insn-asm.h
395
.word 0xE700 | ((v1&15) << 4) | (v3&15)
arch/s390/include/asm/fpu-insn-asm.h
397
MRXBOPC \hint, 0x36, v1, v3
arch/s390/include/asm/fpu-insn-asm.h
435
VX_NUM v3, \vto
arch/s390/include/asm/fpu-insn-asm.h
437
.word 0xE700 | ((v1&15) << 4) | (v3&15)
arch/s390/include/asm/fpu-insn-asm.h
439
MRXBOPC \hint, 0x3E, v1, v3
arch/s390/include/asm/fpu-insn-asm.h
446
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
449
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
450
MRXBOPC (v4&15), 0x8C, v1, v2, v3, v4
arch/s390/include/asm/fpu-insn-asm.h
475
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
477
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
478
MRXBOPC \m4, 0x84, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
484
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
485
.word 0xE700 | ((v1&15) << 4) | (v3&15)
arch/s390/include/asm/fpu-insn-asm.h
487
MRXBOPC \m4, 0x4D, v1, v3
arch/s390/include/asm/fpu-insn-asm.h
506
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
508
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
509
MRXBOPC \m4, 0x61, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
528
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
530
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
531
MRXBOPC \m4, 0x60, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
572
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
574
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
575
MRXBOPC 0, 0x68, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
582
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
584
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
585
MRXBOPC 0, 0x66, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
592
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
594
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
595
MRXBOPC 0, 0x6D, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
602
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
604
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
605
MRXBOPC \m4, 0xB4, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
624
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
627
.word ((v3&15) << 12) | (\m5 << 8)
arch/s390/include/asm/fpu-insn-asm.h
628
MRXBOPC (v4&15), 0xBC, v1, v2, v3, v4
arch/s390/include/asm/fpu-insn-asm.h
647
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
649
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
650
MRXBOPC 0, 0x7D, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
677
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
679
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
680
MRXBOPC \m4, 0xF3, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
702
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
704
.word ((v3&15) << 12)
arch/s390/include/asm/fpu-insn-asm.h
705
MRXBOPC \m4, 0x7A, v1, v2, v3
arch/s390/include/asm/fpu-insn-asm.h
724
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
726
.word 0xE700 | ((v1&15) << 4) | (v3&15)
arch/s390/include/asm/fpu-insn-asm.h
728
MRXBOPC \m4, 0x33, v1, v3
arch/s390/include/asm/fpu-insn-asm.h
747
VX_NUM v3, \vr3
arch/s390/include/asm/fpu-insn-asm.h
749
.word ((v3&15) << 12) | (\imm4)
arch/s390/include/asm/fpu-insn-asm.h
750
MRXBOPC 0, 0x77, v1, v2, v3
arch/s390/include/asm/fpu-insn.h
140
static __always_inline void fpu_vab(u8 v1, u8 v2, u8 v3)
arch/s390/include/asm/fpu-insn.h
144
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3)
arch/s390/include/asm/fpu-insn.h
148
static __always_inline void fpu_vcksm(u8 v1, u8 v2, u8 v3)
arch/s390/include/asm/fpu-insn.h
152
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3)
arch/s390/include/asm/fpu-insn.h
156
static __always_inline void fpu_vesravb(u8 v1, u8 v2, u8 v3)
arch/s390/include/asm/fpu-insn.h
160
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3)
arch/s390/include/asm/fpu-insn.h
164
static __always_inline void fpu_vgfmag(u8 v1, u8 v2, u8 v3, u8 v4)
arch/s390/include/asm/fpu-insn.h
168
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3), [v4] "I" (v4)
arch/s390/include/asm/fpu-insn.h
172
static __always_inline void fpu_vgfmg(u8 v1, u8 v2, u8 v3)
arch/s390/include/asm/fpu-insn.h
176
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3)
arch/s390/include/asm/fpu-insn.h
284
[v1] "I" (_v1), [v3] "I" (_v3) \
arch/s390/include/asm/fpu-insn.h
304
[v1] "I" (_v1), [v3] "I" (_v3) \
arch/s390/include/asm/fpu-insn.h
327
static __always_inline void fpu_vn(u8 v1, u8 v2, u8 v3)
arch/s390/include/asm/fpu-insn.h
331
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3)
arch/s390/include/asm/fpu-insn.h
335
static __always_inline void fpu_vperm(u8 v1, u8 v2, u8 v3, u8 v4)
arch/s390/include/asm/fpu-insn.h
339
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3), [v4] "I" (v4)
arch/s390/include/asm/fpu-insn.h
351
static __always_inline void fpu_vsrlb(u8 v1, u8 v2, u8 v3)
arch/s390/include/asm/fpu-insn.h
355
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3)
arch/s390/include/asm/fpu-insn.h
431
: [v1] "I" (_v1), [v3] "I" (_v3) \
arch/s390/include/asm/fpu-insn.h
450
: [v1] "I" (_v1), [v3] "I" (_v3) \
arch/s390/include/asm/fpu-insn.h
465
static __always_inline void fpu_vx(u8 v1, u8 v2, u8 v3)
arch/s390/include/asm/fpu-insn.h
469
: [v1] "I" (v1), [v2] "I" (v2), [v3] "I" (v3)
arch/um/drivers/cow_user.c
115
struct cow_header_v3 v3;
arch/um/drivers/cow_user.c
338
else if (version == 3 && (*((int*)header->v3.backing_file) != 0)) {
arch/um/drivers/cow_user.c
339
if (n < sizeof(header->v3)) {
arch/um/drivers/cow_user.c
344
*mtime_out = be32toh(header->v3.mtime);
arch/um/drivers/cow_user.c
345
*size_out = be64toh(header->v3.size);
arch/um/drivers/cow_user.c
346
*sectorsize_out = be32toh(header->v3.sectorsize);
arch/um/drivers/cow_user.c
347
*align_out = be32toh(header->v3.alignment);
arch/um/drivers/cow_user.c
352
*bitmap_offset_out = ROUND_UP(sizeof(header->v3), *align_out);
arch/um/drivers/cow_user.c
353
file = header->v3.backing_file;
drivers/clocksource/acpi_pm.c
47
u32 v1 = 0, v2 = 0, v3 = 0;
drivers/clocksource/acpi_pm.c
58
v3 = read_pmtmr();
drivers/clocksource/acpi_pm.c
59
} while (unlikely((v1 > v2 && v1 < v3) || (v2 > v3 && v2 < v1)
drivers/clocksource/acpi_pm.c
60
|| (v3 > v1 && v3 < v2)));
drivers/clocksource/sh_cmt.c
315
u32 v1, v2, v3;
drivers/clocksource/sh_cmt.c
325
v3 = sh_cmt_read_cmcnt(ch);
drivers/clocksource/sh_cmt.c
327
} while (unlikely((o1 != o2) || (v1 > v2 && v1 < v3)
drivers/clocksource/sh_cmt.c
328
|| (v2 > v3 && v2 < v1) || (v3 > v1 && v3 < v2)));
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1008
struct _COMPUTE_MEMORY_ENGINE_PLL_PARAMETERS_V3 v3;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1038
args.v3.ulClockParams = cpu_to_le32((clock_type << 24) | clock);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1044
dividers->post_div = args.v3.ucPostDiv;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1045
dividers->enable_post_div = (args.v3.ucCntlFlag &
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1047
dividers->enable_dithen = (args.v3.ucCntlFlag &
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1049
dividers->whole_fb_div = le16_to_cpu(args.v3.ulFbDiv.usFbDiv);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1050
dividers->frac_fb_div = le16_to_cpu(args.v3.ulFbDiv.usFbDivFrac);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1051
dividers->ref_div = args.v3.ucRefDiv;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1052
dividers->vco_mode = (args.v3.ucCntlFlag &
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1217
struct _SET_VOLTAGE_PARAMETERS_V1_3 v3;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1245
args.v3.ucVoltageType = voltage_type;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1246
args.v3.ucVoltageMode = ATOM_GET_VOLTAGE_LEVEL;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1247
args.v3.usVoltageLevel = cpu_to_le16(voltage_id);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1253
*voltage = le16_to_cpu(args.v3.usVoltageLevel);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1273
struct _ATOM_VOLTAGE_OBJECT_INFO_V3_1 v3;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1279
union _ATOM_VOLTAGE_OBJECT_V3 v3;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1283
static ATOM_VOLTAGE_OBJECT_V3 *amdgpu_atombios_lookup_voltage_object_v3(ATOM_VOLTAGE_OBJECT_INFO_V3_1 *v3,
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1286
u32 size = le16_to_cpu(v3->sHeader.usStructureSize);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1288
u8 *start = (u8 *)v3;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1320
amdgpu_atombios_lookup_voltage_object_v3(&voltage_info->v3,
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1324
*svd_gpio_id = voltage_object->v3.asSVID2Obj.ucSVDGpioId;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1325
*svc_gpio_id = voltage_object->v3.asSVID2Obj.ucSVCGpioId;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1362
if (amdgpu_atombios_lookup_voltage_object_v3(&voltage_info->v3,
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1401
amdgpu_atombios_lookup_voltage_object_v3(&voltage_info->v3,
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
1405
&voltage_object->v3.asGpioVoltageObj;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
896
struct _ATOM_ASIC_SS_ASSIGNMENT_V3 v3;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
974
if ((ss_assign->v3.ucClockIndication == id) &&
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
975
(clock <= le32_to_cpu(ss_assign->v3.ulTargetClockRange))) {
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
977
le16_to_cpu(ss_assign->v3.usSpreadSpectrumPercentage);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
978
ss->type = ss_assign->v3.ucSpreadSpectrumMode;
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
979
ss->rate = le16_to_cpu(ss_assign->v3.usSpreadRateIn10Hz);
drivers/gpu/drm/amd/amdgpu/amdgpu_atombios.c
980
if (ss_assign->v3.ucSpreadSpectrumMode &
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
237
ENABLE_SPREAD_SPECTRUM_ON_PPLL_V3 v3;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
277
args.v3.usSpreadSpectrumAmountFrac = cpu_to_le16(0);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
278
args.v3.ucSpreadSpectrumType = ss->type & ATOM_SS_CENTRE_SPREAD_MODE_MASK;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
281
args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P1PLL;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
284
args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P2PLL;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
287
args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_DCPLL;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
292
args.v3.usSpreadSpectrumAmount = cpu_to_le16(ss->amount);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
293
args.v3.usSpreadSpectrumStep = cpu_to_le16(ss->step);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
294
args.v3.ucEnable = enable;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
301
ADJUST_DISPLAY_PLL_PS_ALLOCATION_V3 v3;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
402
args.v3.sInput.usPixelClock = cpu_to_le16(clock / 10);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
403
args.v3.sInput.ucTransmitterID = amdgpu_encoder->encoder_id;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
404
args.v3.sInput.ucEncodeMode = encoder_mode;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
405
args.v3.sInput.ucDispPllConfig = 0;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
407
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
410
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
413
args.v3.sInput.usPixelClock = cpu_to_le16(dp_clock / 10);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
417
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
420
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
425
args.v3.sInput.ucExtTransmitterID =
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
428
args.v3.sInput.ucExtTransmitterID = 0;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
432
adjusted_clock = le32_to_cpu(args.v3.sOutput.ulDispPllFreq) * 10;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
433
if (args.v3.sOutput.ucRefDiv) {
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
436
amdgpu_crtc->pll_reference_div = args.v3.sOutput.ucRefDiv;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
438
if (args.v3.sOutput.ucPostDiv) {
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
441
amdgpu_crtc->pll_post_div = args.v3.sOutput.ucPostDiv;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
461
PIXEL_CLOCK_PARAMETERS_V3 v3;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
627
args.v3.usPixelClock = cpu_to_le16(clock / 10);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
628
args.v3.usRefDiv = cpu_to_le16(ref_div);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
629
args.v3.usFbDiv = cpu_to_le16(fb_div);
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
630
args.v3.ucFracFbDiv = frac_fb_div;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
631
args.v3.ucPostDiv = post_div;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
632
args.v3.ucPpll = pll_id;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
634
args.v3.ucMiscInfo = PIXEL_CLOCK_MISC_CRTC_SEL_CRTC2;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
636
args.v3.ucMiscInfo = PIXEL_CLOCK_MISC_CRTC_SEL_CRTC1;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
638
args.v3.ucMiscInfo |= PIXEL_CLOCK_MISC_REF_DIV_SRC;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
639
args.v3.ucTransmitterId = encoder_id;
drivers/gpu/drm/amd/amdgpu/atombios_crtc.c
640
args.v3.ucEncoderMode = encoder_mode;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1186
EXTERNAL_ENCODER_CONTROL_PS_ALLOCATION_V3 v3;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1251
args.v3.sExtEncoder.ucAction = action;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1253
args.v3.sExtEncoder.usConnectorId = cpu_to_le16(connector_object_id);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1255
args.v3.sExtEncoder.usPixelClock = cpu_to_le16(amdgpu_encoder->pixel_clock / 10);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1256
args.v3.sExtEncoder.ucEncoderMode =
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1259
if (ENCODER_MODE_IS_DP(args.v3.sExtEncoder.ucEncoderMode)) {
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1261
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_DPLINKRATE_2_70GHZ;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1263
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_DPLINKRATE_5_40GHZ;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1264
args.v3.sExtEncoder.ucLaneNum = dp_lane_count;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1266
args.v3.sExtEncoder.ucLaneNum = 8;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1268
args.v3.sExtEncoder.ucLaneNum = 4;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1271
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_ENCODER1;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1274
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_ENCODER2;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1277
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_ENCODER3;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1280
args.v3.sExtEncoder.ucBitPerColor = amdgpu_atombios_encoder_get_bpc(encoder);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1429
SELECT_CRTC_SOURCE_PARAMETERS_V3 v3;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1561
args.v3.ucCRTC = amdgpu_crtc->crtc_id;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1576
args.v3.ucDstBpc = amdgpu_atombios_encoder_get_bpc(encoder);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1586
args.v3.ucEncoderID = ASIC_INT_DIG1_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1589
args.v3.ucEncoderID = ASIC_INT_DIG2_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1592
args.v3.ucEncoderID = ASIC_INT_DIG3_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1595
args.v3.ucEncoderID = ASIC_INT_DIG4_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1598
args.v3.ucEncoderID = ASIC_INT_DIG5_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1601
args.v3.ucEncoderID = ASIC_INT_DIG6_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1604
args.v3.ucEncoderID = ASIC_INT_DIG7_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1609
args.v3.ucEncoderID = ASIC_INT_DVO_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1613
args.v3.ucEncoderID = ASIC_INT_TV_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1615
args.v3.ucEncoderID = ASIC_INT_TV_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1617
args.v3.ucEncoderID = ASIC_INT_DAC1_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1621
args.v3.ucEncoderID = ASIC_INT_TV_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1623
args.v3.ucEncoderID = ASIC_INT_TV_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
1625
args.v3.ucEncoderID = ASIC_INT_DAC2_ENCODER_ID;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
554
DIG_ENCODER_CONTROL_PARAMETERS_V3 v3;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
601
args.v3.ucPanelMode = panel_mode;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
633
args.v3.ucAction = action;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
634
args.v3.usPixelClock = cpu_to_le16(amdgpu_encoder->pixel_clock / 10);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
636
args.v3.ucPanelMode = panel_mode;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
638
args.v3.ucEncoderMode = amdgpu_atombios_encoder_get_encoder_mode(encoder);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
640
if (ENCODER_MODE_IS_DP(args.v3.ucEncoderMode))
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
641
args.v3.ucLaneNum = dp_lane_count;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
643
args.v3.ucLaneNum = 8;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
645
args.v3.ucLaneNum = 4;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
647
if (ENCODER_MODE_IS_DP(args.v3.ucEncoderMode) && (dp_clock == 270000))
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
649
args.v3.acConfig.ucDigSel = dig->dig_encoder;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
650
args.v3.ucBitPerColor = amdgpu_atombios_encoder_get_bpc(encoder);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
742
DIG_TRANSMITTER_CONTROL_PARAMETERS_V3 v3;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
904
args.v3.ucAction = action;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
906
args.v3.usInitInfo = cpu_to_le16(connector_object_id);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
908
args.v3.asMode.ucLaneSel = lane_num;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
909
args.v3.asMode.ucLaneSet = lane_set;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
912
args.v3.usPixelClock = cpu_to_le16(dp_clock / 10);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
914
args.v3.usPixelClock = cpu_to_le16((amdgpu_encoder->pixel_clock / 2) / 10);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
916
args.v3.usPixelClock = cpu_to_le16(amdgpu_encoder->pixel_clock / 10);
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
920
args.v3.ucLaneNum = dp_lane_count;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
922
args.v3.ucLaneNum = 8;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
924
args.v3.ucLaneNum = 4;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
927
args.v3.acConfig.ucLinkSel = 1;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
929
args.v3.acConfig.ucEncoderSel = 1;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
937
args.v3.acConfig.ucRefClkSource = 2; /* external src */
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
939
args.v3.acConfig.ucRefClkSource = pll_id;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
943
args.v3.acConfig.ucTransmitterSel = 0;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
946
args.v3.acConfig.ucTransmitterSel = 1;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
949
args.v3.acConfig.ucTransmitterSel = 2;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
954
args.v3.acConfig.fCoherentMode = 1; /* DP requires coherent */
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
957
args.v3.acConfig.fCoherentMode = 1;
drivers/gpu/drm/amd/amdgpu/atombios_encoders.c
959
args.v3.acConfig.fDualLinkConnector = 1;
drivers/gpu/drm/amd/display/dc/dml/calcs/dcn_calc_math.c
101
return dcn_bw_max3(v1, v2, v3) > dcn_bw_max2(v4, v5) ? dcn_bw_max3(v1, v2, v3) : dcn_bw_max2(v4, v5);
drivers/gpu/drm/amd/display/dc/dml/calcs/dcn_calc_math.c
94
float dcn_bw_max3(float v1, float v2, float v3)
drivers/gpu/drm/amd/display/dc/dml/calcs/dcn_calc_math.c
96
return v3 > dcn_bw_max2(v1, v2) ? v3 : dcn_bw_max2(v1, v2);
drivers/gpu/drm/amd/display/dc/dml/calcs/dcn_calc_math.c
99
float dcn_bw_max5(float v1, float v2, float v3, float v4, float v5)
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.c
69
double math_max3(double v1, double v2, double v3)
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.c
71
return v3 > math_max2(v1, v2) ? v3 : math_max2(v1, v2);
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.c
74
double math_max4(double v1, double v2, double v3, double v4)
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.c
76
return v4 > math_max3(v1, v2, v3) ? v4 : math_max3(v1, v2, v3);
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.c
79
double math_max5(double v1, double v2, double v3, double v4, double v5)
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.c
81
return math_max3(v1, v2, v3) > math_max2(v4, v5) ? math_max3(v1, v2, v3) : math_max2(v4, v5);
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.h
15
double math_max3(double v1, double v2, double v3);
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.h
16
double math_max4(double v1, double v2, double v3, double v4);
drivers/gpu/drm/amd/display/dc/dml2_0/dml21/src/dml2_standalone_libraries/lib_float_math.h
17
double math_max5(double v1, double v2, double v3, double v4, double v5);
drivers/gpu/drm/amd/display/dc/inc/bw_fixed.h
56
struct bw_fixed v3)
drivers/gpu/drm/amd/display/dc/inc/bw_fixed.h
58
return bw_min2(bw_min2(v1, v2), v3);
drivers/gpu/drm/amd/display/dc/inc/bw_fixed.h
63
struct bw_fixed v3)
drivers/gpu/drm/amd/display/dc/inc/bw_fixed.h
65
return bw_max2(bw_max2(v1, v2), v3);
drivers/gpu/drm/amd/display/dc/inc/dcn_calc_math.h
37
float dcn_bw_max3(float v1, float v2, float v3);
drivers/gpu/drm/amd/display/dc/inc/dcn_calc_math.h
38
float dcn_bw_max5(float v1, float v2, float v3, float v4, float v5);
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
104
#define REG_SET_7(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
109
FN(reg, f3), v3,\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
115
#define REG_SET_8(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
120
FN(reg, f3), v3,\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
127
#define REG_SET_9(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, f5, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
132
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
140
#define REG_SET_10(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, f5, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
145
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
165
#define REG_GET_3(reg_name, f1, v1, f2, v2, f3, v3) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
169
FN(reg_name, f3), v3)
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
171
#define REG_GET_4(reg_name, f1, v1, f2, v2, f3, v3, f4, v4) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
175
FN(reg_name, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
178
#define REG_GET_5(reg_name, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
182
FN(reg_name, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
186
#define REG_GET_6(reg_name, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
190
FN(reg_name, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
195
#define REG_GET_7(reg_name, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
199
FN(reg_name, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
205
#define REG_GET_8(reg_name, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7, f8, v8) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
209
FN(reg_name, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
239
#define REG_UPDATE_3(reg, f1, v1, f2, v2, f3, v3) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
243
FN(reg, f3), v3)
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
245
#define REG_UPDATE_4(reg, f1, v1, f2, v2, f3, v3, f4, v4) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
249
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
252
#define REG_UPDATE_5(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
256
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
260
#define REG_UPDATE_6(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
264
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
269
#define REG_UPDATE_7(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
273
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
279
#define REG_UPDATE_8(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7, f8, v8) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
283
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
290
#define REG_UPDATE_9(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7, f8, v8, f9, v9) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
294
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
302
#define REG_UPDATE_10(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7, f8, v8, f9, v9, f10, v10)\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
306
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
315
#define REG_UPDATE_14(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7, f8, v8, f9, v9, f10,\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
320
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
333
#define REG_UPDATE_19(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7, f8, v8, f9, v9, f10,\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
338
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
356
#define REG_UPDATE_20(reg, f1, v1, f2, v2, f3, v3, f4, v4, f5, v5, f6, v6, f7, v7, f8, v8, f9, v9, f10,\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
361
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
386
#define REG_UPDATE_SEQ_3(reg, f1, v1, f2, v2, f3, v3) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
389
REG_SET(reg, val, f3, v3); }
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
72
#define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
76
FN(reg, f3), v3)
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
78
#define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
82
FN(reg, f3), v3,\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
85
#define REG_SET_5(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
90
FN(reg, f3), v3,\
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
94
#define REG_SET_6(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4, \
drivers/gpu/drm/amd/display/dc/inc/reg_helper.h
99
FN(reg, f3), v3,\
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
101
FN(reg, f3), v3)
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
103
#define REG_UPDATE_4(reg, f1, v1, f2, v2, f3, v3, f4, v4) \
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
107
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
70
#define REG_SET_3(reg, init_value, f1, v1, f2, v2, f3, v3) \
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
74
FN(reg, f3), v3)
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
76
#define REG_SET_4(reg, init_value, f1, v1, f2, v2, f3, v3, f4, v4) \
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
80
FN(reg, f3), v3, \
drivers/gpu/drm/amd/display/dmub/src/dmub_reg.h
97
#define REG_UPDATE_3(reg, f1, v1, f2, v2, f3, v3) \
drivers/gpu/drm/amd/pm/powerplay/hwmgr/ppatomctrl.c
258
return (ATOM_VOLTAGE_OBJECT_INFO *) &(voltage_info->v3);
drivers/gpu/drm/amd/pm/powerplay/hwmgr/ppatomctrl.c
43
struct _ATOM_VOLTAGE_OBJECT_INFO_V3_1 v3;
drivers/gpu/drm/i915/display/intel_dmc.c
1075
const struct intel_dmc_header_v3 *v3 =
drivers/gpu/drm/i915/display/intel_dmc.c
1081
mmioaddr = v3->mmioaddr;
drivers/gpu/drm/i915/display/intel_dmc.c
1082
mmiodata = v3->mmiodata;
drivers/gpu/drm/i915/display/intel_dmc.c
1083
mmio_count = v3->mmio_count;
drivers/gpu/drm/i915/display/intel_dmc.c
1087
start_mmioaddr = v3->start_mmioaddr;
drivers/gpu/drm/i915/display/intel_dmc.c
1088
dmc_header_size = sizeof(*v3);
drivers/gpu/drm/nouveau/nvkm/subdev/gsp/fwsec.c
107
dmemmap->v3.init_cmd = init_cmd;
drivers/gpu/drm/nouveau/nvkm/subdev/gsp/fwsec.c
109
frtscmd = (void *)(dmem + dmemmap->v3.cmd_in_buffer_offset);
drivers/gpu/drm/nouveau/nvkm/subdev/gsp/fwsec.c
168
} v3;
drivers/gpu/drm/nouveau/nvkm/subdev/gsp/fwsec.c
293
case 3: ret = nvkm_gsp_fwsec_v3(gsp, name, &desc->v3, size, init_cmd, fw); break;
drivers/gpu/drm/nouveau/nvkm/subdev/gsp/fwsec.c
67
} v3;
drivers/gpu/drm/radeon/atombios_crtc.c
440
ENABLE_SPREAD_SPECTRUM_ON_PPLL_V3 v3;
drivers/gpu/drm/radeon/atombios_crtc.c
481
args.v3.usSpreadSpectrumAmountFrac = cpu_to_le16(0);
drivers/gpu/drm/radeon/atombios_crtc.c
482
args.v3.ucSpreadSpectrumType = ss->type & ATOM_SS_CENTRE_SPREAD_MODE_MASK;
drivers/gpu/drm/radeon/atombios_crtc.c
485
args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P1PLL;
drivers/gpu/drm/radeon/atombios_crtc.c
488
args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_P2PLL;
drivers/gpu/drm/radeon/atombios_crtc.c
491
args.v3.ucSpreadSpectrumType |= ATOM_PPLL_SS_TYPE_V3_DCPLL;
drivers/gpu/drm/radeon/atombios_crtc.c
496
args.v3.usSpreadSpectrumAmount = cpu_to_le16(ss->amount);
drivers/gpu/drm/radeon/atombios_crtc.c
497
args.v3.usSpreadSpectrumStep = cpu_to_le16(ss->step);
drivers/gpu/drm/radeon/atombios_crtc.c
498
args.v3.ucEnable = enable;
drivers/gpu/drm/radeon/atombios_crtc.c
554
ADJUST_DISPLAY_PLL_PS_ALLOCATION_V3 v3;
drivers/gpu/drm/radeon/atombios_crtc.c
699
args.v3.sInput.usPixelClock = cpu_to_le16(clock / 10);
drivers/gpu/drm/radeon/atombios_crtc.c
700
args.v3.sInput.ucTransmitterID = radeon_encoder->encoder_id;
drivers/gpu/drm/radeon/atombios_crtc.c
701
args.v3.sInput.ucEncodeMode = encoder_mode;
drivers/gpu/drm/radeon/atombios_crtc.c
702
args.v3.sInput.ucDispPllConfig = 0;
drivers/gpu/drm/radeon/atombios_crtc.c
704
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/radeon/atombios_crtc.c
707
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/radeon/atombios_crtc.c
710
args.v3.sInput.usPixelClock = cpu_to_le16(dp_clock / 10);
drivers/gpu/drm/radeon/atombios_crtc.c
714
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/radeon/atombios_crtc.c
717
args.v3.sInput.ucDispPllConfig |=
drivers/gpu/drm/radeon/atombios_crtc.c
722
args.v3.sInput.ucExtTransmitterID =
drivers/gpu/drm/radeon/atombios_crtc.c
725
args.v3.sInput.ucExtTransmitterID = 0;
drivers/gpu/drm/radeon/atombios_crtc.c
729
adjusted_clock = le32_to_cpu(args.v3.sOutput.ulDispPllFreq) * 10;
drivers/gpu/drm/radeon/atombios_crtc.c
730
if (args.v3.sOutput.ucRefDiv) {
drivers/gpu/drm/radeon/atombios_crtc.c
733
radeon_crtc->pll_reference_div = args.v3.sOutput.ucRefDiv;
drivers/gpu/drm/radeon/atombios_crtc.c
735
if (args.v3.sOutput.ucPostDiv) {
drivers/gpu/drm/radeon/atombios_crtc.c
738
radeon_crtc->pll_post_div = args.v3.sOutput.ucPostDiv;
drivers/gpu/drm/radeon/atombios_crtc.c
758
PIXEL_CLOCK_PARAMETERS_V3 v3;
drivers/gpu/drm/radeon/atombios_crtc.c
867
args.v3.usPixelClock = cpu_to_le16(clock / 10);
drivers/gpu/drm/radeon/atombios_crtc.c
868
args.v3.usRefDiv = cpu_to_le16(ref_div);
drivers/gpu/drm/radeon/atombios_crtc.c
869
args.v3.usFbDiv = cpu_to_le16(fb_div);
drivers/gpu/drm/radeon/atombios_crtc.c
870
args.v3.ucFracFbDiv = frac_fb_div;
drivers/gpu/drm/radeon/atombios_crtc.c
871
args.v3.ucPostDiv = post_div;
drivers/gpu/drm/radeon/atombios_crtc.c
872
args.v3.ucPpll = pll_id;
drivers/gpu/drm/radeon/atombios_crtc.c
874
args.v3.ucMiscInfo = PIXEL_CLOCK_MISC_CRTC_SEL_CRTC2;
drivers/gpu/drm/radeon/atombios_crtc.c
876
args.v3.ucMiscInfo = PIXEL_CLOCK_MISC_CRTC_SEL_CRTC1;
drivers/gpu/drm/radeon/atombios_crtc.c
878
args.v3.ucMiscInfo |= PIXEL_CLOCK_MISC_REF_DIV_SRC;
drivers/gpu/drm/radeon/atombios_crtc.c
879
args.v3.ucTransmitterId = encoder_id;
drivers/gpu/drm/radeon/atombios_crtc.c
880
args.v3.ucEncoderMode = encoder_mode;
drivers/gpu/drm/radeon/atombios_encoders.c
1177
args.v3.ucAction = action;
drivers/gpu/drm/radeon/atombios_encoders.c
1179
args.v3.usInitInfo = cpu_to_le16(connector_object_id);
drivers/gpu/drm/radeon/atombios_encoders.c
1181
args.v3.asMode.ucLaneSel = lane_num;
drivers/gpu/drm/radeon/atombios_encoders.c
1182
args.v3.asMode.ucLaneSet = lane_set;
drivers/gpu/drm/radeon/atombios_encoders.c
1185
args.v3.usPixelClock = cpu_to_le16(dp_clock / 10);
drivers/gpu/drm/radeon/atombios_encoders.c
1187
args.v3.usPixelClock = cpu_to_le16((radeon_encoder->pixel_clock / 2) / 10);
drivers/gpu/drm/radeon/atombios_encoders.c
1189
args.v3.usPixelClock = cpu_to_le16(radeon_encoder->pixel_clock / 10);
drivers/gpu/drm/radeon/atombios_encoders.c
1193
args.v3.ucLaneNum = dp_lane_count;
drivers/gpu/drm/radeon/atombios_encoders.c
1195
args.v3.ucLaneNum = 8;
drivers/gpu/drm/radeon/atombios_encoders.c
1197
args.v3.ucLaneNum = 4;
drivers/gpu/drm/radeon/atombios_encoders.c
1200
args.v3.acConfig.ucLinkSel = 1;
drivers/gpu/drm/radeon/atombios_encoders.c
1202
args.v3.acConfig.ucEncoderSel = 1;
drivers/gpu/drm/radeon/atombios_encoders.c
1210
args.v3.acConfig.ucRefClkSource = 2; /* external src */
drivers/gpu/drm/radeon/atombios_encoders.c
1212
args.v3.acConfig.ucRefClkSource = pll_id;
drivers/gpu/drm/radeon/atombios_encoders.c
1216
args.v3.acConfig.ucTransmitterSel = 0;
drivers/gpu/drm/radeon/atombios_encoders.c
1219
args.v3.acConfig.ucTransmitterSel = 1;
drivers/gpu/drm/radeon/atombios_encoders.c
1222
args.v3.acConfig.ucTransmitterSel = 2;
drivers/gpu/drm/radeon/atombios_encoders.c
1227
args.v3.acConfig.fCoherentMode = 1; /* DP requires coherent */
drivers/gpu/drm/radeon/atombios_encoders.c
1230
args.v3.acConfig.fCoherentMode = 1;
drivers/gpu/drm/radeon/atombios_encoders.c
1232
args.v3.acConfig.fDualLinkConnector = 1;
drivers/gpu/drm/radeon/atombios_encoders.c
1419
EXTERNAL_ENCODER_CONTROL_PS_ALLOCATION_V3 v3;
drivers/gpu/drm/radeon/atombios_encoders.c
1483
args.v3.sExtEncoder.ucAction = action;
drivers/gpu/drm/radeon/atombios_encoders.c
1485
args.v3.sExtEncoder.usConnectorId = cpu_to_le16(connector_object_id);
drivers/gpu/drm/radeon/atombios_encoders.c
1487
args.v3.sExtEncoder.usPixelClock = cpu_to_le16(radeon_encoder->pixel_clock / 10);
drivers/gpu/drm/radeon/atombios_encoders.c
1488
args.v3.sExtEncoder.ucEncoderMode = atombios_get_encoder_mode(encoder);
drivers/gpu/drm/radeon/atombios_encoders.c
1490
if (ENCODER_MODE_IS_DP(args.v3.sExtEncoder.ucEncoderMode)) {
drivers/gpu/drm/radeon/atombios_encoders.c
1492
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_DPLINKRATE_2_70GHZ;
drivers/gpu/drm/radeon/atombios_encoders.c
1494
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_DPLINKRATE_5_40GHZ;
drivers/gpu/drm/radeon/atombios_encoders.c
1495
args.v3.sExtEncoder.ucLaneNum = dp_lane_count;
drivers/gpu/drm/radeon/atombios_encoders.c
1497
args.v3.sExtEncoder.ucLaneNum = 8;
drivers/gpu/drm/radeon/atombios_encoders.c
1499
args.v3.sExtEncoder.ucLaneNum = 4;
drivers/gpu/drm/radeon/atombios_encoders.c
1502
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_ENCODER1;
drivers/gpu/drm/radeon/atombios_encoders.c
1505
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_ENCODER2;
drivers/gpu/drm/radeon/atombios_encoders.c
1508
args.v3.sExtEncoder.ucConfig |= EXTERNAL_ENCODER_CONFIG_V3_ENCODER3;
drivers/gpu/drm/radeon/atombios_encoders.c
1511
args.v3.sExtEncoder.ucBitPerColor = radeon_atom_get_bpc(encoder);
drivers/gpu/drm/radeon/atombios_encoders.c
826
DIG_ENCODER_CONTROL_PARAMETERS_V3 v3;
drivers/gpu/drm/radeon/atombios_encoders.c
880
args.v3.ucPanelMode = panel_mode;
drivers/gpu/drm/radeon/atombios_encoders.c
914
args.v3.ucAction = action;
drivers/gpu/drm/radeon/atombios_encoders.c
915
args.v3.usPixelClock = cpu_to_le16(radeon_encoder->pixel_clock / 10);
drivers/gpu/drm/radeon/atombios_encoders.c
917
args.v3.ucPanelMode = panel_mode;
drivers/gpu/drm/radeon/atombios_encoders.c
919
args.v3.ucEncoderMode = atombios_get_encoder_mode(encoder);
drivers/gpu/drm/radeon/atombios_encoders.c
921
if (ENCODER_MODE_IS_DP(args.v3.ucEncoderMode))
drivers/gpu/drm/radeon/atombios_encoders.c
922
args.v3.ucLaneNum = dp_lane_count;
drivers/gpu/drm/radeon/atombios_encoders.c
924
args.v3.ucLaneNum = 8;
drivers/gpu/drm/radeon/atombios_encoders.c
926
args.v3.ucLaneNum = 4;
drivers/gpu/drm/radeon/atombios_encoders.c
928
if (ENCODER_MODE_IS_DP(args.v3.ucEncoderMode) && (dp_clock == 270000))
drivers/gpu/drm/radeon/atombios_encoders.c
931
args.v3.acConfig.ucDigSel = enc_override;
drivers/gpu/drm/radeon/atombios_encoders.c
933
args.v3.acConfig.ucDigSel = dig->dig_encoder;
drivers/gpu/drm/radeon/atombios_encoders.c
934
args.v3.ucBitPerColor = radeon_atom_get_bpc(encoder);
drivers/gpu/drm/radeon/atombios_encoders.c
995
DIG_TRANSMITTER_CONTROL_PARAMETERS_V3 v3;
drivers/gpu/drm/radeon/radeon_atombios.c
1502
struct _ATOM_ASIC_SS_ASSIGNMENT_V3 v3;
drivers/gpu/drm/radeon/radeon_atombios.c
1580
if ((ss_assign->v3.ucClockIndication == id) &&
drivers/gpu/drm/radeon/radeon_atombios.c
1581
(clock <= le32_to_cpu(ss_assign->v3.ulTargetClockRange))) {
drivers/gpu/drm/radeon/radeon_atombios.c
1583
le16_to_cpu(ss_assign->v3.usSpreadSpectrumPercentage);
drivers/gpu/drm/radeon/radeon_atombios.c
1584
ss->type = ss_assign->v3.ucSpreadSpectrumMode;
drivers/gpu/drm/radeon/radeon_atombios.c
1585
ss->rate = le16_to_cpu(ss_assign->v3.usSpreadRateIn10Hz);
drivers/gpu/drm/radeon/radeon_atombios.c
1586
if (ss_assign->v3.ucSpreadSpectrumMode &
drivers/gpu/drm/radeon/radeon_atombios.c
2818
struct _COMPUTE_MEMORY_ENGINE_PLL_PARAMETERS_V3 v3;
drivers/gpu/drm/radeon/radeon_atombios.c
2874
args.v3.ulClockParams = cpu_to_le32((clock_type << 24) | clock);
drivers/gpu/drm/radeon/radeon_atombios.c
2878
dividers->post_div = args.v3.ucPostDiv;
drivers/gpu/drm/radeon/radeon_atombios.c
2879
dividers->enable_post_div = (args.v3.ucCntlFlag &
drivers/gpu/drm/radeon/radeon_atombios.c
2881
dividers->enable_dithen = (args.v3.ucCntlFlag &
drivers/gpu/drm/radeon/radeon_atombios.c
2883
dividers->whole_fb_div = le16_to_cpu(args.v3.ulFbDiv.usFbDiv);
drivers/gpu/drm/radeon/radeon_atombios.c
2884
dividers->frac_fb_div = le16_to_cpu(args.v3.ulFbDiv.usFbDivFrac);
drivers/gpu/drm/radeon/radeon_atombios.c
2885
dividers->ref_div = args.v3.ucRefDiv;
drivers/gpu/drm/radeon/radeon_atombios.c
2886
dividers->vco_mode = (args.v3.ucCntlFlag &
drivers/gpu/drm/radeon/radeon_atombios.c
3092
struct _SET_VOLTAGE_PARAMETERS_V1_3 v3;
drivers/gpu/drm/radeon/radeon_atombios.c
3120
args.v3.ucVoltageType = voltage_type;
drivers/gpu/drm/radeon/radeon_atombios.c
3121
args.v3.ucVoltageMode = ATOM_SET_VOLTAGE;
drivers/gpu/drm/radeon/radeon_atombios.c
3122
args.v3.usVoltageLevel = cpu_to_le16(voltage_level);
drivers/gpu/drm/radeon/radeon_atombios.c
3155
args.v3.ucVoltageType = voltage_type;
drivers/gpu/drm/radeon/radeon_atombios.c
3156
args.v3.ucVoltageMode = ATOM_GET_VOLTAGE_LEVEL;
drivers/gpu/drm/radeon/radeon_atombios.c
3157
args.v3.usVoltageLevel = cpu_to_le16(voltage_id);
drivers/gpu/drm/radeon/radeon_atombios.c
3161
*voltage = le16_to_cpu(args.v3.usVoltageLevel);
drivers/gpu/drm/radeon/radeon_atombios.c
3191
args.v3.ucVoltageType = 0;
drivers/gpu/drm/radeon/radeon_atombios.c
3192
args.v3.ucVoltageMode = ATOM_GET_LEAKAGE_ID;
drivers/gpu/drm/radeon/radeon_atombios.c
3193
args.v3.usVoltageLevel = 0;
drivers/gpu/drm/radeon/radeon_atombios.c
3197
*leakage_id = le16_to_cpu(args.v3.usVoltageLevel);
drivers/gpu/drm/radeon/radeon_atombios.c
3371
struct _ATOM_VOLTAGE_OBJECT_INFO_V3_1 v3;
drivers/gpu/drm/radeon/radeon_atombios.c
3377
union _ATOM_VOLTAGE_OBJECT_V3 v3;
drivers/gpu/drm/radeon/radeon_atombios.c
3414
static ATOM_VOLTAGE_OBJECT_V3 *atom_lookup_voltage_object_v3(ATOM_VOLTAGE_OBJECT_INFO_V3_1 *v3,
drivers/gpu/drm/radeon/radeon_atombios.c
3417
u32 size = le16_to_cpu(v3->sHeader.usStructureSize);
drivers/gpu/drm/radeon/radeon_atombios.c
3419
u8 *start = (u8 *)v3;
drivers/gpu/drm/radeon/radeon_atombios.c
3472
if (atom_lookup_voltage_object_v3(&voltage_info->v3,
drivers/gpu/drm/radeon/radeon_atombios.c
3510
atom_lookup_voltage_object_v3(&voltage_info->v3,
drivers/gpu/drm/radeon/radeon_atombios.c
3514
*svd_gpio_id = voltage_object->v3.asSVID2Obj.ucSVDGpioId;
drivers/gpu/drm/radeon/radeon_atombios.c
3515
*svc_gpio_id = voltage_object->v3.asSVID2Obj.ucSVCGpioId;
drivers/gpu/drm/radeon/radeon_atombios.c
3769
atom_lookup_voltage_object_v3(&voltage_info->v3,
drivers/gpu/drm/radeon/radeon_atombios.c
3773
&voltage_object->v3.asGpioVoltageObj;
drivers/media/platform/rockchip/rkisp1/rkisp1-regs.h
392
#define RKISP1_CIF_ISP_HIST_WEIGHT_SET_V10(v0, v1, v2, v3) \
drivers/media/platform/rockchip/rkisp1/rkisp1-regs.h
395
(((v3) & 0x1f) << 24))
drivers/media/platform/rockchip/rkisp1/rkisp1-regs.h
422
#define RKISP1_CIF_ISP_HIST_WEIGHT_SET_V12(v0, v1, v2, v3) \
drivers/media/platform/rockchip/rkisp1/rkisp1-regs.h
425
(((v3) & 0x3f) << 24))
drivers/net/ethernet/chelsio/cxgb3/mc5.c
101
u32 v3)
drivers/net/ethernet/chelsio/cxgb3/mc5.c
105
t3_write_reg(adapter, A_MC5_DB_DBGI_REQ_DATA2, v3);
drivers/net/wireless/broadcom/b43legacy/main.c
418
u16 v3;
drivers/net/wireless/broadcom/b43legacy/main.c
424
v3 = b43legacy_read16(dev, B43legacy_MMIO_TSF_3);
drivers/net/wireless/broadcom/b43legacy/main.c
432
} while (v3 != test3 || v2 != test2 || v1 != test1);
drivers/net/wireless/broadcom/b43legacy/main.c
434
*tsf = v3;
drivers/net/wireless/broadcom/b43legacy/main.c
483
u16 v3 = (tsf & 0xFFFF000000000000ULL) >> 48;
drivers/net/wireless/broadcom/b43legacy/main.c
486
b43legacy_write16(dev, B43legacy_MMIO_TSF_3, v3);
drivers/net/wireless/broadcom/b43legacy/phy.c
1759
s8 v3;
drivers/net/wireless/broadcom/b43legacy/phy.c
1787
v3 = (s8)((tmp & 0xFF00) >> 8);
drivers/net/wireless/broadcom/b43legacy/phy.c
1790
if (v0 == 0x7F || v1 == 0x7F || v2 == 0x7F || v3 == 0x7F) {
drivers/net/wireless/broadcom/b43legacy/phy.c
1798
v3 = (s8)((tmp & 0xFF00) >> 8);
drivers/net/wireless/broadcom/b43legacy/phy.c
1799
if (v0 == 0x7F || v1 == 0x7F || v2 == 0x7F || v3 == 0x7F)
drivers/net/wireless/broadcom/b43legacy/phy.c
1804
v3 = (v3 + 0x20) & 0x3F;
drivers/net/wireless/broadcom/b43legacy/phy.c
1809
average = (v0 + v1 + v2 + v3 + 2) / 4;
drivers/net/wireless/broadcom/brcm80211/brcmsmac/phy/phy_n.c
21241
u16 v0 = 0x211, v1 = 0x222, v2 = 0x144, v3 = 0x188;
drivers/net/wireless/broadcom/brcm80211/brcmsmac/phy/phy_n.c
21254
1, 0x0C, 16, &v3);
drivers/net/wireless/broadcom/brcm80211/brcmsmac/phy/phy_n.c
21265
1, 0x1C, 16, &v3);
drivers/net/wireless/intel/iwlwifi/fw/api/nvm-reg.h
488
struct iwl_tas_config_cmd_v3 v3;
drivers/net/wireless/intel/iwlwifi/fw/api/power.h
381
struct iwl_dev_tx_power_cmd_v3 v3;
drivers/net/wireless/intel/iwlwifi/fw/api/power.h
530
struct iwl_geo_tx_power_profiles_cmd_v3 v3;
drivers/net/wireless/intel/iwlwifi/fw/api/rx.h
729
struct iwl_rx_mpdu_desc_v3 v3;
drivers/net/wireless/intel/iwlwifi/mld/debugfs.c
1014
size_t count, void *data, bool v3)
drivers/net/wireless/intel/iwlwifi/mld/debugfs.c
1037
rate = iwl_v3_rate_from_v2_v3(cpu_to_le32(rate), v3);
drivers/net/wireless/intel/iwlwifi/mld/rx.c
1775
u16 hwsum = be16_to_cpu(mpdu_desc->v3.raw_xsum);
drivers/net/wireless/intel/iwlwifi/mld/rx.c
2084
mpdu_desc->v3.channel);
drivers/net/wireless/intel/iwlwifi/mld/rx.c
2108
le64_to_cpu(mpdu_desc->v3.tsf_on_air_rise);
drivers/net/wireless/intel/iwlwifi/mld/rx.c
42
phy_data->rate_n_flags = iwl_v3_rate_from_v2_v3(desc->v3.rate_n_flags,
drivers/net/wireless/intel/iwlwifi/mld/rx.c
44
phy_data->gp2_on_air_rise = le32_to_cpu(desc->v3.gp2_on_air_rise);
drivers/net/wireless/intel/iwlwifi/mld/rx.c
45
phy_data->energy_a = desc->v3.energy_a;
drivers/net/wireless/intel/iwlwifi/mld/rx.c
46
phy_data->energy_b = desc->v3.energy_b;
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
1001
cmd.v3.table_revision = sk;
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
1154
cmd_size = sizeof(cmd_v2_v4.common) + sizeof(cmd_v2_v4.v3);
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
1155
cmd_v2_v4.v3.override_tas_iec =
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
1157
cmd_v2_v4.v3.enable_tas_iec =
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
881
len = sizeof(cmd.v3);
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
883
per_chain = cmd.v3.per_chain[0][0];
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
931
len = sizeof(geo_tx_cmd.v3);
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
998
len = sizeof(cmd.v3);
drivers/net/wireless/intel/iwlwifi/mvm/fw.c
999
n_bands = ARRAY_SIZE(cmd.v3.table[0]);
drivers/net/wireless/intel/iwlwifi/mvm/mac80211.c
1489
len = sizeof(cmd.v3);
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2126
iwl_mvm_v3_rate_from_fw(desc->v3.rate_n_flags,
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2128
phy_data.channel = desc->v3.channel;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2129
phy_data.gp2_on_air_rise = le32_to_cpu(desc->v3.gp2_on_air_rise);
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2130
phy_data.energy_a = desc->v3.energy_a;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2131
phy_data.energy_b = desc->v3.energy_b;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2133
phy_data.d0 = desc->v3.phy_data0;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2134
phy_data.d1 = desc->v3.phy_data1;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2135
phy_data.d2 = desc->v3.phy_data2;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2136
phy_data.d3 = desc->v3.phy_data3;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2138
phy_data.d5 = desc->v3.phy_data5;
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
2210
tsf_on_air_rise = le64_to_cpu(desc->v3.tsf_on_air_rise);
drivers/net/wireless/intel/iwlwifi/mvm/rxmq.c
523
u16 hwsum = be16_to_cpu(desc->v3.raw_xsum);
drivers/net/wireless/mediatek/mt76/mt76x02_phy.c
51
mt76x02_tx_power_mask(u8 v1, u8 v2, u8 v3, u8 v4)
drivers/net/wireless/mediatek/mt76/mt76x02_phy.c
57
val |= (v3 & (BIT(6) - 1)) << 16;
drivers/net/wireless/mediatek/mt76/mt7915/mac.c
890
bool v3, wake = false;
drivers/net/wireless/mediatek/mt76/mt7915/mac.c
898
v3 = (FIELD_GET(MT_TX_FREE_VER, txd) == 0x4);
drivers/net/wireless/mediatek/mt76/mt7915/mac.c
930
if (v3 && (info & MT_TX_FREE_MPDU_HEADER_V3)) {
drivers/net/wireless/mediatek/mt76/mt7915/mac.c
935
} else if (!v3 && (info & MT_TX_FREE_MPDU_HEADER)) {
drivers/net/wireless/mediatek/mt76/mt7915/mac.c
945
if (v3 && (info & MT_TX_FREE_MPDU_HEADER_V3))
drivers/net/wireless/mediatek/mt76/mt7915/mac.c
948
for (i = 0; i < 1 + v3; i++) {
drivers/net/wireless/mediatek/mt76/mt7915/mac.c
949
if (v3) {
drivers/net/wireless/mediatek/mt76/mt7925/mac.c
511
u32 v3;
drivers/net/wireless/mediatek/mt76/mt7925/mac.c
519
v3 = le32_to_cpu(rxv[3]);
drivers/net/wireless/mediatek/mt76/mt7925/mac.c
522
status->chain_signal[0] = to_rssi(MT_PRXV_RCPI0, v3);
drivers/net/wireless/mediatek/mt76/mt7925/mac.c
523
status->chain_signal[1] = to_rssi(MT_PRXV_RCPI1, v3);
drivers/net/wireless/mediatek/mt76/mt7925/mac.c
524
status->chain_signal[2] = to_rssi(MT_PRXV_RCPI2, v3);
drivers/net/wireless/mediatek/mt76/mt7925/mac.c
525
status->chain_signal[3] = to_rssi(MT_PRXV_RCPI3, v3);
drivers/net/wireless/mediatek/mt76/mt7996/mac.c
617
u32 v3;
drivers/net/wireless/mediatek/mt76/mt7996/mac.c
625
v3 = le32_to_cpu(rxv[3]);
drivers/net/wireless/mediatek/mt76/mt7996/mac.c
628
status->chain_signal[0] = to_rssi(MT_PRXV_RCPI0, v3);
drivers/net/wireless/mediatek/mt76/mt7996/mac.c
629
status->chain_signal[1] = to_rssi(MT_PRXV_RCPI1, v3);
drivers/net/wireless/mediatek/mt76/mt7996/mac.c
630
status->chain_signal[2] = to_rssi(MT_PRXV_RCPI2, v3);
drivers/net/wireless/mediatek/mt76/mt7996/mac.c
631
status->chain_signal[3] = to_rssi(MT_PRXV_RCPI3, v3);
drivers/net/wireless/realtek/rtlwifi/rtl8192ee/phy.c
858
u32 v1 = 0, v2 = 0, v3 = 0, v4 = 0, v5 = 0, v6 = 0;
drivers/net/wireless/realtek/rtlwifi/rtl8192ee/phy.c
867
v3 = phy_regarray_table_pg[i+2];
drivers/net/wireless/realtek/rtlwifi/rtl8192ee/phy.c
873
_rtl92ee_store_tx_power_by_rate(hw, v1, v2, v3,
drivers/net/wireless/realtek/rtlwifi/rtl8723be/phy.c
712
u32 v1 = 0, v2 = 0, v3 = 0, v4 = 0, v5 = 0, v6 = 0;
drivers/net/wireless/realtek/rtlwifi/rtl8723be/phy.c
721
v3 = phy_regarray_table_pg[i+2];
drivers/net/wireless/realtek/rtlwifi/rtl8723be/phy.c
732
v1, v2, v3, v4, v5, v6);
drivers/net/wireless/realtek/rtlwifi/rtl8821ae/phy.c
1984
u32 v1, v2, v3, v4, v5, v6;
drivers/net/wireless/realtek/rtlwifi/rtl8821ae/phy.c
2002
v3 = array[i+2];
drivers/net/wireless/realtek/rtlwifi/rtl8821ae/phy.c
2028
_rtl8821ae_store_tx_power_by_rate(hw, v1, v2, v3,
drivers/net/wireless/realtek/rtw89/coex.c
10686
pstep = &pfwinfo->rpt_fbtc_step.finfo.v3;
drivers/net/wireless/realtek/rtw89/coex.c
1491
pfinfo = &pfwinfo->rpt_fbtc_tdma.finfo.v3;
drivers/net/wireless/realtek/rtw89/coex.c
1492
pcinfo->req_len = sizeof(pfwinfo->rpt_fbtc_tdma.finfo.v3);
drivers/net/wireless/realtek/rtw89/coex.c
1493
fwsubver->fcxtdma = pfwinfo->rpt_fbtc_tdma.finfo.v3.fver;
drivers/net/wireless/realtek/rtw89/coex.c
1523
pfinfo = &pfwinfo->rpt_fbtc_cysta.finfo.v3;
drivers/net/wireless/realtek/rtw89/coex.c
1524
pcysta->v3 = pfwinfo->rpt_fbtc_cysta.finfo.v3;
drivers/net/wireless/realtek/rtw89/coex.c
1525
pcinfo->req_len = sizeof(pfwinfo->rpt_fbtc_cysta.finfo.v3);
drivers/net/wireless/realtek/rtw89/coex.c
1526
fwsubver->fcxcysta = pfwinfo->rpt_fbtc_cysta.finfo.v3.fver;
drivers/net/wireless/realtek/rtw89/coex.c
1559
pfinfo = &pfwinfo->rpt_fbtc_step.finfo.v3;
drivers/net/wireless/realtek/rtw89/coex.c
1560
pcinfo->req_len = sizeof(pfwinfo->rpt_fbtc_step.finfo.v3.step[0]) *
drivers/net/wireless/realtek/rtw89/coex.c
1563
fwsubver->fcxstep = pfwinfo->rpt_fbtc_step.finfo.v3.fver;
drivers/net/wireless/realtek/rtw89/coex.c
1901
&pfwinfo->rpt_fbtc_tdma.finfo.v3.tdma,
drivers/net/wireless/realtek/rtw89/coex.c
1966
if (le16_to_cpu(pcysta->v3.cycles) < BTC_CYSTA_CHK_PERIOD)
drivers/net/wireless/realtek/rtw89/coex.c
1969
cnt_leak_slot = le32_to_cpu(pcysta->v3.slot_cnt[CXST_LK]);
drivers/net/wireless/realtek/rtw89/coex.c
1970
cnt_rx_imr = le32_to_cpu(pcysta->v3.leak_slot.cnt_rximr);
drivers/net/wireless/realtek/rtw89/coex.c
1985
wl_slot_real = le16_to_cpu(pcysta->v3.cycle_time.tavg[CXT_WL]);
drivers/net/wireless/realtek/rtw89/coex.c
1996
bt_slot_real = le16_to_cpu(pcysta->v3.cycle_time.tavg[CXT_BT]);
drivers/net/wireless/realtek/rtw89/coex.c
2004
le32_to_cpu(pcysta->v3.slot_cnt[CXST_W1]));
drivers/net/wireless/realtek/rtw89/coex.c
2006
le32_to_cpu(pcysta->v3.slot_cnt[CXST_B1]));
drivers/net/wireless/realtek/rtw89/coex.c
2008
le16_to_cpu(pcysta->v3.cycles));
drivers/net/wireless/realtek/rtw89/coex.c
2227
struct rtw89_btc_fbtc_tdma_v3 *v3;
drivers/net/wireless/realtek/rtw89/coex.c
2253
tlv->len = sizeof(*v3);
drivers/net/wireless/realtek/rtw89/coex.c
2254
v3 = (struct rtw89_btc_fbtc_tdma_v3 *)&tlv->val[0];
drivers/net/wireless/realtek/rtw89/coex.c
2255
v3->fver = ver->fcxtdma;
drivers/net/wireless/realtek/rtw89/coex.c
2256
v3->tdma = dm->tdma;
drivers/net/wireless/realtek/rtw89/coex.c
2257
btc->policy_len += BTC_TLV_HDR_LEN + sizeof(*v3);
drivers/net/wireless/realtek/rtw89/coex.c
9675
pcysta->v3 = pfwinfo->rpt_fbtc_cysta.finfo.v3;
drivers/net/wireless/realtek/rtw89/coex.c
9676
except_cnt = le32_to_cpu(pcysta->v3.except_cnt);
drivers/net/wireless/realtek/rtw89/coex.c
9677
exception_map = le32_to_cpu(pcysta->v3.except_map);
drivers/net/wireless/realtek/rtw89/coex.c
9745
t = &pfwinfo->rpt_fbtc_tdma.finfo.v3.tdma;
drivers/net/wireless/realtek/rtw89/coex.c
9958
pcysta = &pfwinfo->rpt_fbtc_cysta.finfo.v3;
drivers/net/wireless/realtek/rtw89/core.h
2228
struct rtw89_btc_fbtc_tdma_v3 v3;
drivers/net/wireless/realtek/rtw89/core.h
2652
struct rtw89_btc_fbtc_steps_v3 v3;
drivers/net/wireless/realtek/rtw89/core.h
2877
struct rtw89_btc_fbtc_cysta_v3 v3;
drivers/net/wireless/realtek/rtw89/rtw8922a.c
1186
s8 v1, v2, v3;
drivers/net/wireless/realtek/rtw89/rtw8922a.c
1198
v3 = clamp_t(s32, value, S8_MIN, S8_MAX);
drivers/net/wireless/realtek/rtw89/rtw8922a.c
1202
rtw89_phy_write32_mask(rtwdev, rpl_ext_comp[path], 0xff00, v3);
drivers/net/wireless/realtek/rtw89/rtw8922a.c
1206
rtw89_phy_write32_mask(rtwdev, rssi_tb_ext_comp[path], 0xff000000, v3);
drivers/pci/controller/pci-hyperv.c
1897
struct pci_create_interrupt3 v3;
drivers/pci/controller/pci-hyperv.c
1999
size = hv_compose_msi_req_v3(&ctxt.int_pkts.v3,
drivers/pci/controller/pci-v3-semi.c
313
struct v3_pci *v3 = bus->sysdata;
drivers/pci/controller/pci-v3-semi.c
365
writel(v3_addr_to_lb_base(v3->non_pre_mem) |
drivers/pci/controller/pci-v3-semi.c
367
v3->base + V3_LB_BASE0);
drivers/pci/controller/pci-v3-semi.c
373
writel(v3_addr_to_lb_base(v3->config_mem) |
drivers/pci/controller/pci-v3-semi.c
375
v3->base + V3_LB_BASE1);
drivers/pci/controller/pci-v3-semi.c
376
writew(mapaddress, v3->base + V3_LB_MAP1);
drivers/pci/controller/pci-v3-semi.c
378
return v3->config_base + address + offset;
drivers/pci/controller/pci-v3-semi.c
381
static void v3_unmap_bus(struct v3_pci *v3)
drivers/pci/controller/pci-v3-semi.c
386
writel(v3_addr_to_lb_base(v3->pre_mem) |
drivers/pci/controller/pci-v3-semi.c
389
v3->base + V3_LB_BASE1);
drivers/pci/controller/pci-v3-semi.c
390
writew(v3_addr_to_lb_map(v3->pre_bus_addr) |
drivers/pci/controller/pci-v3-semi.c
392
v3->base + V3_LB_MAP1);
drivers/pci/controller/pci-v3-semi.c
397
writel(v3_addr_to_lb_base(v3->non_pre_mem) |
drivers/pci/controller/pci-v3-semi.c
399
v3->base + V3_LB_BASE0);
drivers/pci/controller/pci-v3-semi.c
405
struct v3_pci *v3 = bus->sysdata;
drivers/pci/controller/pci-v3-semi.c
412
v3_unmap_bus(v3);
drivers/pci/controller/pci-v3-semi.c
419
struct v3_pci *v3 = bus->sysdata;
drivers/pci/controller/pci-v3-semi.c
426
v3_unmap_bus(v3);
drivers/pci/controller/pci-v3-semi.c
438
struct v3_pci *v3 = data;
drivers/pci/controller/pci-v3-semi.c
439
struct device *dev = v3->dev;
drivers/pci/controller/pci-v3-semi.c
442
status = readw(v3->base + V3_PCI_STAT);
drivers/pci/controller/pci-v3-semi.c
451
writew(status, v3->base + V3_PCI_STAT);
drivers/pci/controller/pci-v3-semi.c
453
status = readb(v3->base + V3_LB_ISTAT);
drivers/pci/controller/pci-v3-semi.c
471
writeb(0, v3->base + V3_LB_ISTAT);
drivers/pci/controller/pci-v3-semi.c
472
if (v3->map)
drivers/pci/controller/pci-v3-semi.c
473
regmap_write(v3->map, INTEGRATOR_SC_PCI_OFFSET,
drivers/pci/controller/pci-v3-semi.c
480
static int v3_integrator_init(struct v3_pci *v3)
drivers/pci/controller/pci-v3-semi.c
484
v3->map =
drivers/pci/controller/pci-v3-semi.c
486
if (IS_ERR(v3->map)) {
drivers/pci/controller/pci-v3-semi.c
487
dev_err(v3->dev, "no syscon\n");
drivers/pci/controller/pci-v3-semi.c
491
regmap_read(v3->map, INTEGRATOR_SC_PCI_OFFSET, &val);
drivers/pci/controller/pci-v3-semi.c
493
regmap_write(v3->map, INTEGRATOR_SC_PCI_OFFSET,
drivers/pci/controller/pci-v3-semi.c
502
writel(0x6200, v3->base + V3_LB_IO_BASE);
drivers/pci/controller/pci-v3-semi.c
506
writeb(0xaa, v3->base + V3_MAIL_DATA);
drivers/pci/controller/pci-v3-semi.c
507
writeb(0x55, v3->base + V3_MAIL_DATA + 4);
drivers/pci/controller/pci-v3-semi.c
508
} while (readb(v3->base + V3_MAIL_DATA) != 0xaa &&
drivers/pci/controller/pci-v3-semi.c
509
readb(v3->base + V3_MAIL_DATA) != 0x55);
drivers/pci/controller/pci-v3-semi.c
512
dev_info(v3->dev, "initialized PCI V3 Integrator/AP integration\n");
drivers/pci/controller/pci-v3-semi.c
517
static int v3_pci_setup_resource(struct v3_pci *v3,
drivers/pci/controller/pci-v3-semi.c
521
struct device *dev = v3->dev;
drivers/pci/controller/pci-v3-semi.c
532
v3->base + V3_LB_BASE2);
drivers/pci/controller/pci-v3-semi.c
534
v3->base + V3_LB_MAP2);
drivers/pci/controller/pci-v3-semi.c
540
v3->pre_mem = mem->start;
drivers/pci/controller/pci-v3-semi.c
541
v3->pre_bus_addr = mem->start - win->offset;
drivers/pci/controller/pci-v3-semi.c
543
mem, &v3->pre_bus_addr);
drivers/pci/controller/pci-v3-semi.c
548
if (v3->non_pre_mem &&
drivers/pci/controller/pci-v3-semi.c
549
(mem->start != v3->non_pre_mem + SZ_256M)) {
drivers/pci/controller/pci-v3-semi.c
555
writel(v3_addr_to_lb_base(v3->pre_mem) |
drivers/pci/controller/pci-v3-semi.c
559
v3->base + V3_LB_BASE1);
drivers/pci/controller/pci-v3-semi.c
560
writew(v3_addr_to_lb_map(v3->pre_bus_addr) |
drivers/pci/controller/pci-v3-semi.c
562
v3->base + V3_LB_MAP1);
drivers/pci/controller/pci-v3-semi.c
565
v3->non_pre_mem = mem->start;
drivers/pci/controller/pci-v3-semi.c
566
v3->non_pre_bus_addr = mem->start - win->offset;
drivers/pci/controller/pci-v3-semi.c
568
mem, &v3->non_pre_bus_addr);
drivers/pci/controller/pci-v3-semi.c
575
writel(v3_addr_to_lb_base(v3->non_pre_mem) |
drivers/pci/controller/pci-v3-semi.c
578
v3->base + V3_LB_BASE0);
drivers/pci/controller/pci-v3-semi.c
579
writew(v3_addr_to_lb_map(v3->non_pre_bus_addr) |
drivers/pci/controller/pci-v3-semi.c
581
v3->base + V3_LB_MAP0);
drivers/pci/controller/pci-v3-semi.c
595
static int v3_get_dma_range_config(struct v3_pci *v3,
drivers/pci/controller/pci-v3-semi.c
599
struct device *dev = v3->dev;
drivers/pci/controller/pci-v3-semi.c
657
dev_err(v3->dev, "illegal dma memory chunk size\n");
drivers/pci/controller/pci-v3-semi.c
673
static int v3_pci_parse_map_dma_ranges(struct v3_pci *v3,
drivers/pci/controller/pci-v3-semi.c
676
struct pci_host_bridge *bridge = pci_host_bridge_from_priv(v3);
drivers/pci/controller/pci-v3-semi.c
677
struct device *dev = v3->dev;
drivers/pci/controller/pci-v3-semi.c
685
ret = v3_get_dma_range_config(v3, entry, &pci_base, &pci_map);
drivers/pci/controller/pci-v3-semi.c
690
writel(pci_base, v3->base + V3_PCI_BASE0);
drivers/pci/controller/pci-v3-semi.c
691
writel(pci_map, v3->base + V3_PCI_MAP0);
drivers/pci/controller/pci-v3-semi.c
693
writel(pci_base, v3->base + V3_PCI_BASE1);
drivers/pci/controller/pci-v3-semi.c
694
writel(pci_map, v3->base + V3_PCI_MAP1);
drivers/pci/controller/pci-v3-semi.c
710
struct v3_pci *v3;
drivers/pci/controller/pci-v3-semi.c
717
host = devm_pci_alloc_host_bridge(dev, sizeof(*v3));
drivers/pci/controller/pci-v3-semi.c
722
v3 = pci_host_bridge_priv(host);
drivers/pci/controller/pci-v3-semi.c
723
host->sysdata = v3;
drivers/pci/controller/pci-v3-semi.c
724
v3->dev = dev;
drivers/pci/controller/pci-v3-semi.c
738
v3->base = devm_platform_get_and_ioremap_resource(pdev, 0, &regs);
drivers/pci/controller/pci-v3-semi.c
739
if (IS_ERR(v3->base))
drivers/pci/controller/pci-v3-semi.c
740
return PTR_ERR(v3->base);
drivers/pci/controller/pci-v3-semi.c
746
if (readl(v3->base + V3_LB_IO_BASE) != (regs->start >> 16))
drivers/pci/controller/pci-v3-semi.c
748
readl(v3->base + V3_LB_IO_BASE), regs);
drivers/pci/controller/pci-v3-semi.c
756
v3->config_mem = regs->start;
drivers/pci/controller/pci-v3-semi.c
757
v3->config_base = devm_ioremap_resource(dev, regs);
drivers/pci/controller/pci-v3-semi.c
758
if (IS_ERR(v3->config_base))
drivers/pci/controller/pci-v3-semi.c
759
return PTR_ERR(v3->config_base);
drivers/pci/controller/pci-v3-semi.c
767
"PCIv3 error", v3);
drivers/pci/controller/pci-v3-semi.c
778
if (readw(v3->base + V3_SYSTEM) & V3_SYSTEM_M_LOCK)
drivers/pci/controller/pci-v3-semi.c
779
writew(V3_SYSTEM_UNLOCK, v3->base + V3_SYSTEM);
drivers/pci/controller/pci-v3-semi.c
782
val = readw(v3->base + V3_PCI_CMD);
drivers/pci/controller/pci-v3-semi.c
784
writew(val, v3->base + V3_PCI_CMD);
drivers/pci/controller/pci-v3-semi.c
787
val = readw(v3->base + V3_SYSTEM);
drivers/pci/controller/pci-v3-semi.c
789
writew(val, v3->base + V3_SYSTEM);
drivers/pci/controller/pci-v3-semi.c
792
val = readw(v3->base + V3_PCI_CFG);
drivers/pci/controller/pci-v3-semi.c
794
writew(val, v3->base + V3_PCI_CFG);
drivers/pci/controller/pci-v3-semi.c
797
val = readw(v3->base + V3_LB_CFG);
drivers/pci/controller/pci-v3-semi.c
802
writew(val, v3->base + V3_LB_CFG);
drivers/pci/controller/pci-v3-semi.c
805
val = readw(v3->base + V3_PCI_CMD);
drivers/pci/controller/pci-v3-semi.c
807
writew(val, v3->base + V3_PCI_CMD);
drivers/pci/controller/pci-v3-semi.c
811
ret = v3_pci_setup_resource(v3, host, win);
drivers/pci/controller/pci-v3-semi.c
817
ret = v3_pci_parse_map_dma_ranges(v3, np);
drivers/pci/controller/pci-v3-semi.c
826
writel(0x00000000, v3->base + V3_PCI_IO_BASE);
drivers/pci/controller/pci-v3-semi.c
834
writew(val, v3->base + V3_PCI_CFG);
drivers/pci/controller/pci-v3-semi.c
845
v3->base + V3_FIFO_PRIORITY);
drivers/pci/controller/pci-v3-semi.c
852
writeb(0, v3->base + V3_LB_ISTAT);
drivers/pci/controller/pci-v3-semi.c
853
val = readw(v3->base + V3_LB_CFG);
drivers/pci/controller/pci-v3-semi.c
855
writew(val, v3->base + V3_LB_CFG);
drivers/pci/controller/pci-v3-semi.c
857
v3->base + V3_LB_IMASK);
drivers/pci/controller/pci-v3-semi.c
861
ret = v3_integrator_init(v3);
drivers/pci/controller/pci-v3-semi.c
867
val = readw(v3->base + V3_PCI_CMD);
drivers/pci/controller/pci-v3-semi.c
869
writew(val, v3->base + V3_PCI_CMD);
drivers/pci/controller/pci-v3-semi.c
872
writeb(0, v3->base + V3_LB_ISTAT);
drivers/pci/controller/pci-v3-semi.c
875
v3->base + V3_LB_IMASK);
drivers/pci/controller/pci-v3-semi.c
878
val = readw(v3->base + V3_SYSTEM);
drivers/pci/controller/pci-v3-semi.c
880
writew(val, v3->base + V3_SYSTEM);
drivers/pci/controller/pci-v3-semi.c
885
val = readw(v3->base + V3_SYSTEM);
drivers/pci/controller/pci-v3-semi.c
887
writew(val, v3->base + V3_SYSTEM);
drivers/staging/rtl8723bs/hal/HalHWImg8723B_BB.c
551
u32 v3 = Array[i + 2];
drivers/staging/rtl8723bs/hal/HalHWImg8723B_BB.c
554
odm_ConfigBB_PHY_REG_PG_8723B(pDM_Odm, v1, v2, v3, v4);
drivers/ufs/host/ufs-mediatek-sip.h
48
unsigned long v3;
drivers/ufs/host/ufs-mediatek-sip.h
60
s.v1, s.v2, s.v3, s.v4, s.v5, s.v6, s.res);
drivers/video/fbdev/sis/sis_main.c
4321
u8 reg, v1, v2, v3, v4, v5, v6, v7, v8;
drivers/video/fbdev/sis/sis_main.c
4339
v3 = 0x80; v6 = 0x80;
drivers/video/fbdev/sis/sis_main.c
4351
v3 = bios[rindex++];
drivers/video/fbdev/sis/sis_main.c
4360
SiS_SetReg(SISSR, 0x2a, v3);
drivers/video/fbdev/sis/sis_main.c
4372
v1 = 0x01; v2 = 0x43; v3 = 0x1e; v4 = 0x2a;
drivers/video/fbdev/sis/sis_main.c
4378
v3 = bios[memtype + 16];
drivers/video/fbdev/sis/sis_main.c
4386
v3 &= 0xfd;
drivers/video/fbdev/sis/sis_main.c
4389
SiS_SetReg(SISSR, 0x17, v3);
drivers/video/fbdev/sis/sis_main.c
4407
v1 = 0xf6; v2 = 0x0d; v3 = 0x00;
drivers/video/fbdev/sis/sis_main.c
4411
v3 = bios[0xea];
drivers/video/fbdev/sis/sis_main.c
4415
SiS_SetReg(SISSR, 0x25, v3);
drivers/video/fbdev/sis/sis_main.c
4855
u8 v1, v2, v3;
drivers/video/fbdev/sis/sis_main.c
4881
v1 = cs90[index]; v2 = cs90[index + 1]; v3 = cs90[index + 2];
drivers/video/fbdev/sis/sis_main.c
4885
v3 = ivideo->bios_abase[0x90 + index + 2];
drivers/video/fbdev/sis/sis_main.c
4889
SiS_SetReg(SISSR, 0x2a, v3);
drivers/video/fbdev/sis/sis_main.c
4894
v1 = csb8[index]; v2 = csb8[index + 1]; v3 = csb8[index + 2];
drivers/video/fbdev/sis/sis_main.c
4898
v3 = ivideo->bios_abase[0xb8 + index + 2];
drivers/video/fbdev/sis/sis_main.c
4902
SiS_SetReg(SISSR, 0x30, v3);
drivers/video/fbdev/sis/sis_main.c
5004
u8 v3;
drivers/video/fbdev/sis/sis_main.c
5012
v1 = cs168[regb]; v2 = cs160[regb]; v3 = cs158[regb];
drivers/video/fbdev/sis/sis_main.c
5016
v3 = bios[regb + 0x158];
drivers/video/fbdev/sis/sis_main.c
5025
SiS_SetReg(SISCR, 0x82, v3);
drivers/video/fbdev/sis/sis_main.c
5079
u8 v1, v2, v3, v4, v5, reg, ramtype;
drivers/video/fbdev/sis/sis_main.c
5472
v1 = 0xb5; v2 = 0x20; v3 = 0xf0; v4 = 0x13;
drivers/video/fbdev/sis/sis_main.c
5476
v3 = bios[0x120 + regb];
drivers/video/fbdev/sis/sis_main.c
5492
SiS_SetReg(SISCR, 0x59, v3);
drivers/video/fbdev/sis/sis_main.c
5539
v1 = cs158[regb]; v2 = cs160[regb]; v3 = cs168[regb];
drivers/video/fbdev/sis/sis_main.c
5543
v3 = bios[regb + 0x168];
drivers/video/fbdev/sis/sis_main.c
5547
SiS_SetReg(SISCR, 0x86, v3);
drivers/video/fbdev/sis/sis_main.c
5595
v1 = 0x31; v2 = 0x03; v3 = 0x83; v4 = 0x03; v5 = 0x83;
drivers/video/fbdev/sis/sis_main.c
5600
v3 = bios[index + 1];
drivers/video/fbdev/sis/sis_main.c
5607
SiS_SetReg(SISSR, 0x16, v3);
fs/adfs/map.c
262
unsigned int v0, v1, v2, v3;
fs/adfs/map.c
265
v0 = v1 = v2 = v3 = 0;
fs/adfs/map.c
267
v0 += map[i] + (v3 >> 8);
fs/adfs/map.c
268
v3 &= 0xff;
fs/adfs/map.c
273
v3 += map[i + 3] + (v2 >> 8);
fs/adfs/map.c
276
v0 += v3 >> 8;
fs/adfs/map.c
279
v3 += map[3] + (v2 >> 8);
fs/adfs/map.c
281
return v0 ^ v1 ^ v2 ^ v3;
include/crypto/aria.h
332
static inline u32 make_u32(u8 v0, u8 v1, u8 v2, u8 v3)
include/crypto/aria.h
334
return ((u32)v0 << 24) | ((u32)v1 << 16) | ((u32)v2 << 8) | ((u32)v3);
include/linux/xxhash.h
150
uint64_t v3;
include/pcmcia/device_id.h
101
.prod_id = { NULL, NULL, (v3), NULL }, \
include/pcmcia/device_id.h
137
#define PCMCIA_MFC_DEVICE_PROD_ID13(mfc, v1, v3, vh1, vh3) { \
include/pcmcia/device_id.h
141
.prod_id = { (v1), NULL, (v3), NULL }, \
include/pcmcia/device_id.h
145
#define PCMCIA_MFC_DEVICE_PROD_ID123(mfc, v1, v2, v3, vh1, vh2, vh3) { \
include/pcmcia/device_id.h
150
.prod_id = { (v1), (v2), (v3), NULL },\
include/pcmcia/device_id.h
186
#define PCMCIA_PFC_DEVICE_PROD_ID13(mfc, v1, v3, vh1, vh3) { \
include/pcmcia/device_id.h
190
.prod_id = { (v1), NULL, (v3), NULL }, \
include/pcmcia/device_id.h
194
#define PCMCIA_PFC_DEVICE_PROD_ID123(mfc, v1, v2, v3, vh1, vh2, vh3) { \
include/pcmcia/device_id.h
199
.prod_id = { (v1), (v2), (v3), NULL },\
include/pcmcia/device_id.h
221
#define PCMCIA_DEVICE_CIS_PROD_ID123(v1, v2, v3, vh1, vh2, vh3, _cisfile) { \
include/pcmcia/device_id.h
226
.prod_id = { (v1), (v2), (v3), NULL },\
include/pcmcia/device_id.h
34
#define PCMCIA_DEVICE_PROD_ID3(v3, vh3) { \
include/pcmcia/device_id.h
36
.prod_id = { NULL, NULL, (v3), NULL }, \
include/pcmcia/device_id.h
45
#define PCMCIA_DEVICE_PROD_ID13(v1, v3, vh1, vh3) { \
include/pcmcia/device_id.h
48
.prod_id = { (v1), NULL, (v3), NULL }, \
include/pcmcia/device_id.h
57
#define PCMCIA_DEVICE_PROD_ID123(v1, v2, v3, vh1, vh2, vh3) { \
include/pcmcia/device_id.h
61
.prod_id = { (v1), (v2), (v3), NULL },\
include/pcmcia/device_id.h
71
#define PCMCIA_DEVICE_PROD_ID134(v1, v3, v4, vh1, vh3, vh4) { \
include/pcmcia/device_id.h
75
.prod_id = { (v1), NULL, (v3), (v4) }, \
include/pcmcia/device_id.h
78
#define PCMCIA_DEVICE_PROD_ID1234(v1, v2, v3, v4, vh1, vh2, vh3, vh4) { \
include/pcmcia/device_id.h
83
.prod_id = { (v1), (v2), (v3), (v4) }, \
include/pcmcia/device_id.h
95
#define PCMCIA_DEVICE_MANF_CARD_PROD_ID3(manf, card, v3, vh3) { \
lib/atomic64_test.c
152
long long v3 = 0x8000000000000000LL;
lib/atomic64_test.c
243
INIT(v3);
lib/siphash.c
119
v3 ^= first;
lib/siphash.c
136
v3 ^= first;
lib/siphash.c
140
v3 ^= second;
lib/siphash.c
159
v3 ^= first;
lib/siphash.c
163
v3 ^= second;
lib/siphash.c
167
v3 ^= third;
lib/siphash.c
187
v3 ^= first;
lib/siphash.c
191
v3 ^= second;
lib/siphash.c
195
v3 ^= third;
lib/siphash.c
199
v3 ^= forth;
lib/siphash.c
20
#define SIPROUND SIPHASH_PERMUTATION(v0, v1, v2, v3)
lib/siphash.c
220
v3 ^= combined;
lib/siphash.c
237
v3 ^= b; \
lib/siphash.c
244
return (v0 ^ v1) ^ (v2 ^ v3);
lib/siphash.c
255
v3 ^= m;
lib/siphash.c
26
u64 v3 = SIPHASH_CONST_3; \
lib/siphash.c
28
v3 ^= key->key[1]; \
lib/siphash.c
288
v3 ^= m;
lib/siphash.c
334
v3 ^= combined;
lib/siphash.c
34
v3 ^= b; \
lib/siphash.c
353
v3 ^= combined;
lib/siphash.c
374
v3 ^= combined;
lib/siphash.c
378
v3 ^= combined;
lib/siphash.c
385
#define HSIPROUND HSIPHASH_PERMUTATION(v0, v1, v2, v3)
lib/siphash.c
391
u32 v3 = HSIPHASH_CONST_3; \
lib/siphash.c
393
v3 ^= key->key[1]; \
lib/siphash.c
399
v3 ^= b; \
lib/siphash.c
406
return v1 ^ v3;
lib/siphash.c
417
v3 ^= m;
lib/siphash.c
43
return (v0 ^ v1) ^ (v2 ^ v3);
lib/siphash.c
440
v3 ^= m;
lib/siphash.c
461
v3 ^= first;
lib/siphash.c
477
v3 ^= first;
lib/siphash.c
480
v3 ^= second;
lib/siphash.c
498
v3 ^= first;
lib/siphash.c
501
v3 ^= second;
lib/siphash.c
504
v3 ^= third;
lib/siphash.c
523
v3 ^= first;
lib/siphash.c
526
v3 ^= second;
lib/siphash.c
529
v3 ^= third;
lib/siphash.c
532
v3 ^= forth;
lib/siphash.c
54
v3 ^= m;
lib/siphash.c
87
v3 ^= m;
lib/xxhash.c
105
v3 = xxh32_round(v3, get_unaligned_le32(p));
lib/xxhash.c
112
xxh_rotl32(v3, 12) + xxh_rotl32(v4, 18);
lib/xxhash.c
167
uint64_t v3 = seed + 0;
lib/xxhash.c
175
v3 = xxh64_round(v3, get_unaligned_le64(p));
lib/xxhash.c
182
xxh_rotl64(v3, 12) + xxh_rotl64(v4, 18);
lib/xxhash.c
185
h64 = xxh64_merge_round(h64, v3);
lib/xxhash.c
235
state.v3 = seed + 0;
lib/xxhash.c
267
state->v3 = xxh64_round(state->v3, get_unaligned_le64(p64));
lib/xxhash.c
279
uint64_t v3 = state->v3;
lib/xxhash.c
287
v3 = xxh64_round(v3, get_unaligned_le64(p));
lib/xxhash.c
295
state->v3 = v3;
lib/xxhash.c
318
const uint64_t v3 = state->v3;
lib/xxhash.c
322
xxh_rotl64(v3, 12) + xxh_rotl64(v4, 18);
lib/xxhash.c
325
h64 = xxh64_merge_round(h64, v3);
lib/xxhash.c
328
h64 = state->v3 + PRIME64_5;
lib/xxhash.c
97
uint32_t v3 = seed + 0;
sound/usb/clock.c
26
struct uac3_clock_source_descriptor v3;
sound/usb/clock.c
260
bmControls = le32_to_cpu(cs_desc->v3.bmControls);
sound/usb/clock.c
31
struct uac3_clock_selector_descriptor v3;
sound/usb/clock.c
332
bmControls = le32_to_cpu(*(__le32 *)(&selector->v3.baCSourceID[0] + pins));
sound/usb/clock.c
36
struct uac_clock_multiplier_descriptor v3;
sound/usb/clock.c
42
((p)->v3.bLength >= sizeof((p)->v3)) : \
sound/usb/clock.c
46
((proto) == UAC_VERSION_3 ? (p)->v3.field : (p)->v2.field)
sound/usb/clock.c
572
bmControls = le32_to_cpu(cs_desc->v3.bmControls);
sound/usb/clock.c
84
return cs->v3.bLength >= sizeof(cs->v3) + cs->v3.bNrInPins +
tools/power/cpupower/debug/kernel/cpufreq-test_tsc.c
37
u32 v1=0,v2=0,v3=0;
tools/power/cpupower/debug/kernel/cpufreq-test_tsc.c
46
v3 = inl(pm_tmr_ioport);
tools/power/cpupower/debug/kernel/cpufreq-test_tsc.c
47
} while ((v1 > v2 && v1 < v3) || (v2 > v3 && v2 < v1)
tools/power/cpupower/debug/kernel/cpufreq-test_tsc.c
48
|| (v3 > v1 && v3 < v2));
tools/testing/selftests/bpf/progs/test_siphash.h
26
#define SIPROUND SIPHASH_PERMUTATION(v0, v1, v2, v3)
tools/testing/selftests/bpf/progs/test_siphash.h
32
u64 v3 = SIPHASH_CONST_3; \
tools/testing/selftests/bpf/progs/test_siphash.h
34
v3 ^= key->key[1]; \
tools/testing/selftests/bpf/progs/test_siphash.h
40
v3 ^= b; \
tools/testing/selftests/bpf/progs/test_siphash.h
49
return (v0 ^ v1) ^ (v2 ^ v3);
tools/testing/selftests/bpf/progs/test_siphash.h
54
v3 ^= first;
tools/testing/selftests/bpf/progs/test_siphash.h
58
v3 ^= second;
tools/testing/selftests/riscv/vector/v_exec_initval_nolibc.c
57
CHECK_VECTOR_REGISTER(v3);