Home
last modified time | relevance | path

Searched refs:v0 (Results 1 – 25 of 352) sorted by relevance

12345678910>>...15

/linux-6.15/drivers/gpu/drm/nouveau/nvkm/engine/disp/
H A Duoutp.c38 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_dp_mst_vcpi()
43 ior->func->dp->vcpi(ior, args->v0.head, args->v0.start_slot, args->v0.num_slots, in nvkm_uoutp_mthd_dp_mst_vcpi()
44 args->v0.pbn, args->v0.aligned_pbn); in nvkm_uoutp_mthd_dp_mst_vcpi()
53 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_dp_mst_id_put()
66 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_dp_mst_id_get()
91 args->v0.watermark, args->v0.hblanksym, args->v0.vblanksym); in nvkm_uoutp_mthd_dp_sst()
104 return outp->func->dp.drive(outp, args->v0.lanes, args->v0.pe, args->v0.vs); in nvkm_uoutp_mthd_dp_drive()
163 args->v0.data, &args->v0.size); in nvkm_uoutp_mthd_dp_aux_xfer()
268 args->v0.max_ac_packet, args->v0.rekey); in nvkm_uoutp_mthd_hdmi()
270 ior->func->hdmi->scdc(ior, args->v0.khz, args->v0.scdc, args->v0.scdc_scrambling, in nvkm_uoutp_mthd_hdmi()
[all …]
H A Duconn.c38 args.v0.version = 0; in nvkm_uconn_uevent_gsp()
39 args.v0.types = 0; in nvkm_uconn_uevent_gsp()
45 args.v0.types |= NVIF_CONN_EVENT_V0_IRQ; in nvkm_uconn_uevent_gsp()
55 args.v0.version = 0; in nvkm_uconn_uevent_aux()
56 args.v0.types = 0; in nvkm_uconn_uevent_aux()
62 args.v0.types |= NVIF_CONN_EVENT_V0_IRQ; in nvkm_uconn_uevent_aux()
72 args.v0.version = 0; in nvkm_uconn_uevent_gpio()
73 args.v0.types = 0; in nvkm_uconn_uevent_gpio()
110 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uconn_uevent()
177 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uconn_new()
[all …]
H A Duhead.c50 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uhead_mthd_scanoutpos()
54 args->v0.vtotal = head->arm.vtotal; in nvkm_uhead_mthd_scanoutpos()
55 args->v0.vblanks = head->arm.vblanks; in nvkm_uhead_mthd_scanoutpos()
56 args->v0.vblanke = head->arm.vblanke; in nvkm_uhead_mthd_scanoutpos()
57 args->v0.htotal = head->arm.htotal; in nvkm_uhead_mthd_scanoutpos()
58 args->v0.hblanks = head->arm.hblanks; in nvkm_uhead_mthd_scanoutpos()
59 args->v0.hblanke = head->arm.hblanke; in nvkm_uhead_mthd_scanoutpos()
65 if (!args->v0.vtotal || !args->v0.htotal) in nvkm_uhead_mthd_scanoutpos()
68 args->v0.time[0] = ktime_to_ns(ktime_get()); in nvkm_uhead_mthd_scanoutpos()
69 head->func->rgpos(head, &args->v0.hline, &args->v0.vline); in nvkm_uhead_mthd_scanoutpos()
[all …]
/linux-6.15/arch/arm64/crypto/
H A Daes-ce-core.S13 ld1 {v0.16b}, [x2]
23 aesmc v0.16b, v0.16b
26 aesmc v0.16b, v0.16b
30 aesmc v0.16b, v0.16b
34 eor v0.16b, v0.16b, v3.16b
51 aesimc v0.16b, v0.16b
54 aesimc v0.16b, v0.16b
58 aesimc v0.16b, v0.16b
62 eor v0.16b, v0.16b, v3.16b
73 movi v0.16b, #0
[all …]
H A Dsm4-ce-core.S52 rev32 v0.16b, v0.16b;
59 eor v0.16b, v0.16b, v1.16b;
61 sm4ekey v0.4s, v0.4s, v24.4s;
179 eor v0.16b, v0.16b, RIV.16b
395 eor v0.16b, v0.16b, RIV.16b
446 eor v0.16b, v0.16b, v8.16b
478 eor v0.16b, v0.16b, v8.16b
497 eor v0.16b, v0.16b, v8.16b
627 eor v0.16b, v0.16b, v8.16b
631 eor v0.16b, v0.16b, v8.16b
[all …]
H A Daes-modes.S196 eor v0.16b, v0.16b, cbciv.16b
209 eor v0.16b, v0.16b, cbciv.16b
265 tbl v0.16b, {v0.16b}, v3.16b
460 eor v0.16b, v5.16b, v0.16b
661 eor v0.16b, v0.16b, v4.16b
669 eor v0.16b, v0.16b, v4.16b
685 eor v0.16b, v0.16b, v4.16b
687 eor v0.16b, v0.16b, v4.16b
753 eor v0.16b, v0.16b, v4.16b
761 eor v0.16b, v0.16b, v4.16b
[all …]
/linux-6.15/drivers/gpu/drm/nouveau/nvkm/engine/device/
H A Dctrl.c46 args->v0.version); in nvkm_control_mthd_pstate_info()
57 args->v0.count = 0; in nvkm_control_mthd_pstate_info()
60 args->v0.pwrsrc = -ENODEV; in nvkm_control_mthd_pstate_info()
85 args->v0.version, args->v0.state, args->v0.index); in nvkm_control_mthd_pstate_attr()
124 snprintf(args->v0.name, sizeof(args->v0.name), "%s", domain->mname); in nvkm_control_mthd_pstate_attr()
125 snprintf(args->v0.unit, sizeof(args->v0.unit), "MHz"); in nvkm_control_mthd_pstate_attr()
129 args->v0.index = 0; in nvkm_control_mthd_pstate_attr()
132 args->v0.index = ++j; in nvkm_control_mthd_pstate_attr()
153 args->v0.version, args->v0.ustate, args->v0.pwrsrc); in nvkm_control_mthd_pstate_user()
159 if (args->v0.pwrsrc >= 0) { in nvkm_control_mthd_pstate_user()
[all …]
H A Duser.c80 struct nv_device_info_v0 v0; in nvkm_udevice_info() member
152 args->v0.family = 0; in nvkm_udevice_info()
156 args->v0.chipset = device->chipset; in nvkm_udevice_info()
157 args->v0.revision = device->chiprev; in nvkm_udevice_info()
159 args->v0.ram_size = args->v0.ram_user = fb->ram->size; in nvkm_udevice_info()
161 args->v0.ram_size = args->v0.ram_user = 0; in nvkm_udevice_info()
162 if (imem && args->v0.ram_size > 0) in nvkm_udevice_info()
163 args->v0.ram_user = args->v0.ram_user - imem->reserved; in nvkm_udevice_info()
165 snprintf(args->v0.chip, sizeof(args->v0.chip), "%s", device->chip->name); in nvkm_udevice_info()
166 snprintf(args->v0.name, sizeof(args->v0.name), "%s", device->name); in nvkm_udevice_info()
[all …]
/linux-6.15/drivers/gpu/drm/nouveau/nvkm/subdev/mmu/
H A Dummu.c61 struct nvif_mmu_heap_v0 v0; in nvkm_ummu_heap() member
81 struct nvif_mmu_type_v0 v0; in nvkm_ummu_type() member
110 struct nvif_mmu_kind_v0 v0; in nvkm_ummu_kind() member
120 if (argc != args->v0.count * sizeof(*args->v0.data)) in nvkm_ummu_kind()
122 if (args->v0.count > count) in nvkm_ummu_kind()
124 args->v0.kind_inv = kind_inv; in nvkm_ummu_kind()
125 memcpy(args->v0.data, kind, args->v0.count); in nvkm_ummu_kind()
157 struct nvif_mmu_v0 v0; in nvkm_ummu_new() member
169 args->v0.heap_nr = mmu->heap_nr; in nvkm_ummu_new()
170 args->v0.type_nr = mmu->type_nr; in nvkm_ummu_new()
[all …]
H A Duvmm.c56 addr = args->v0.addr; in nvkm_uvmm_mthd_pfnclr()
57 size = args->v0.size; in nvkm_uvmm_mthd_pfnclr()
85 page = args->v0.page; in nvkm_uvmm_mthd_pfnmap()
86 addr = args->v0.addr; in nvkm_uvmm_mthd_pfnmap()
87 size = args->v0.size; in nvkm_uvmm_mthd_pfnmap()
88 phys = args->v0.phys; in nvkm_uvmm_mthd_pfnmap()
118 addr = args->v0.addr; in nvkm_uvmm_mthd_unmap()
164 addr = args->v0.addr; in nvkm_uvmm_mthd_map()
165 size = args->v0.size; in nvkm_uvmm_mthd_map()
243 addr = args->v0.addr; in nvkm_uvmm_mthd_put()
[all …]
/linux-6.15/drivers/gpu/drm/nouveau/nvkm/core/
H A Dioctl.c72 args->v0.version, args->v0.count); in nvkm_ioctl_sclass()
73 if (size != args->v0.count * sizeof(args->v0.oclass[0])) in nvkm_ioctl_sclass()
77 if (i < args->v0.count) { in nvkm_ioctl_sclass()
85 args->v0.count = i; in nvkm_ioctl_sclass()
105 args->v0.version, args->v0.handle, args->v0.oclass, in nvkm_ioctl_new()
106 args->v0.object); in nvkm_ioctl_new()
182 args->v0.version, args->v0.method); in nvkm_ioctl_mthd()
289 struct nvif_ioctl_v0 v0; in nvkm_ioctl() member
298 args->v0.version, args->v0.type, args->v0.object, in nvkm_ioctl()
299 args->v0.owner); in nvkm_ioctl()
[all …]
/linux-6.15/arch/mips/include/asm/mach-cavium-octeon/
H A Dkernel-entry-init.h38 or v0, v0, 0x5001
39 xor v0, v0, 0x1001
43 and v0, v0, v1
44 ori v0, v0, (6 << 7)
64 or v0, v0, 0x2000 # Set IPREF bit.
74 dsll v0, 7
75 beqz v0, 2f
76 1: dsubu v0, 8
78 bnez v0, 1b
86 dli v0, 0x27
[all …]
/linux-6.15/arch/riscv/lib/
H A Dxor.S11 vle8.v v0, (a1)
14 vxor.vv v16, v0, v8
25 vle8.v v0, (a1)
28 vxor.vv v0, v0, v8
42 vle8.v v0, (a1)
45 vxor.vv v0, v0, v8
48 vxor.vv v0, v0, v16
62 vle8.v v0, (a1)
65 vxor.vv v0, v0, v8
68 vxor.vv v0, v0, v16
[all …]
/linux-6.15/drivers/gpu/drm/amd/amdkfd/
H A Dcwsr_trap_handler_gfx10.asm701 v_mbcnt_hi_u32_b32 v0, -1, v0
702 v_mul_u32_u24 v0, 4, v0
823 v_movrels_b32 v0, v0 //v0 = v[0+m0]
838 v_movrels_b32 v0, v0 //v0 = v[0+m0]
868 v_movrels_b32 v0, v0 //v0 = v[0+m0]
883 v_movrels_b32 v0, v0 //v0 = v[0+m0]
915 v_movrels_b32 v0, v0
927 v_movrels_b32 v0, v0 //v0 = v[0+m0]
1050 v_movreld_b32 v0, v0 //v[0+m0] = v0
1084 v_movreld_b32 v0, v0 //v[0+m0] = v0
[all …]
H A Dcwsr_trap_handler_gfx12.asm329 v_mov_b32 v0, 0x0
568 v_mbcnt_hi_u32_b32 v0, -1, v0
569 v_mul_u32_u24 v0, 4, v0
589 v_add_nc_u32 v0, v0, 128 //mem offset increased by 128 bytes
607 v_add_nc_u32 v0, v0, 256 //mem offset increased by 256 bytes
646 v_movrels_b32 v0, v0 //v0 = v[0+m0]
672 v_movrels_b32 v0, v0 //v0 = v[0+m0]
699 v_movrels_b32 v0, v0 //v0 = v[0+m0]
817 v_movreld_b32 v0, v0 //v[0+m0] = v0
851 v_movreld_b32 v0, v0 //v[0+m0] = v0
[all …]
/linux-6.15/tools/testing/selftests/powerpc/math/
H A Dvmx_asm.S15 lvx v0,r5,r4
20 lvx v0,r5,r4
25 lvx v0,r5,r4
30 lvx v0,r5,r4
35 lvx v0,r5,r4
40 lvx v0,r5,r4
45 lvx v0,r5,r4
50 lvx v0,r5,r4
55 lvx v0,r5,r4
60 lvx v0,r5,r4
[all …]
/linux-6.15/drivers/gpu/drm/nouveau/include/nvif/
H A Dif0012.h41 } v0; member
80 } v0; member
89 } v0; member
98 } v0; member
116 } v0; member
138 } v0; member
150 } v0; member
157 } v0; member
165 } v0; member
179 } v0; member
[all …]
/linux-6.15/lib/
H A Dsiphash.c37 v0 ^= b; \
57 v0 ^= m; in __siphash_aligned()
90 v0 ^= m; in __siphash_unaligned()
122 v0 ^= first; in siphash_1u64()
139 v0 ^= first; in siphash_2u64()
239 v0 ^= b; \
257 v0 ^= m; in __hsiphash_aligned()
290 v0 ^= m; in __hsiphash_unaligned()
401 v0 ^= b; \
419 v0 ^= m; in __hsiphash_aligned()
[all …]
H A Datomic64_test.c22 atomic##bit##_set(&v, v0); \
23 r = v0; \
47 r = v0; \
56 r = v0; \
106 int v0 = 0xaaa31337; in test_atomic() local
141 XCHG_FAMILY_TEST(, v0, v1); in test_atomic()
158 long long r = v0; in test_atomic64()
190 INIT(v0); in test_atomic64()
195 INIT(v0); in test_atomic64()
206 INIT(v0); in test_atomic64()
[all …]
/linux-6.15/arch/arm64/lib/
H A Dxor-neon.c30 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_2()
59 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_3()
65 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_3()
97 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_4()
103 v0 = veorq_u64(v0, vld1q_u64(dp4 + 0)); in xor_arm64_neon_4()
109 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_4()
144 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_5()
150 v0 = veorq_u64(v0, vld1q_u64(dp4 + 0)); in xor_arm64_neon_5()
156 v0 = veorq_u64(v0, vld1q_u64(dp5 + 0)); in xor_arm64_neon_5()
255 v0 = veorq_u64(v0, vld1q_u64(dp4 + 0)); in xor_arm64_eor3_4()
[all …]
H A Dcrc-t10dif-core.S223 CPU_LE( rev64 v0.16b, v0.16b )
231 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
243 eor v0.16b, v0.16b, v8.16b
291 CPU_LE( rev64 v0.16b, v0.16b )
292 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
313 CPU_LE( rev64 v0.16b, v0.16b )
314 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
414 eor v0.16b, v0.16b, v7.16b // + low bits * x^64
421 eor v0.16b, v0.16b, v1.16b // + low bits
430 ushr v0.2d, v0.2d, #48
[all …]
/linux-6.15/arch/powerpc/lib/
H A Dcrc32-vpmsum_core.S157 vxor v0,v0,v0
256 vxor v0,v0,v8
313 vxor v0,v0,v8
347 vxor v0,v0,v8
449 vxor v0,v0,v16
456 vxor v0,v0,v16
463 vxor v0,v0,v16
470 vxor v0,v0,v16
499 vxor v0,v0,v2
502 vxor v0,v0,v4
[all …]
/linux-6.15/drivers/gpu/drm/nouveau/nvkm/engine/fifo/
H A Duchan.c50 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uchan_uevent()
53 switch (args->v0.type) { in nvkm_uchan_uevent()
342 if (argc < sizeof(args->v0) || args->v0.version != 0) in nvkm_uchan_new()
344 argc -= sizeof(args->v0); in nvkm_uchan_new()
354 if (args->v0.vmm) { in nvkm_uchan_new()
360 if (args->v0.ctxdma) { in nvkm_uchan_new()
368 if (args->v0.huserd) { in nvkm_uchan_new()
387 args->v0.priv != 0, args->v0.devm, vmm, ctxdma, args->v0.offset, in nvkm_uchan_new()
388 args->v0.length, userd, args->v0.ouserd, &uchan->chan); in nvkm_uchan_new()
398 args->v0.token = ~0; in nvkm_uchan_new()
[all …]
/linux-6.15/arch/mips/lib/
H A Dstrncpy_user.S38 1: EX(lbue, v0, (v1), .Lfault)
41 1: EX(lbu, v0, (v1), .Lfault)
45 sb v0, (a0)
46 beqz v0, 2f
50 2: PTR_ADDU v0, a1, t0
51 xor v0, a1
52 bltz v0, .Lfault
53 move v0, t0
58 li v0, -EFAULT
/linux-6.15/arch/mips/kernel/
H A Dscall32-o32.S89 LONG_S v0, TI_SYSCALL($28) # Save v0 as syscall number
97 subu v0, v0, __NR_O32_Linux # check syscall number
101 sll t0, v0, 2
111 sltu t0, t0, v0
116 negu v0 # error
150 li v0, EFAULT
151 sw v0, PT_R2(sp)
176 li v0, ENOSYS # error
177 sw v0, PT_R2(sp)
188 beqz v0, einval
[all …]

12345678910>>...15