Home
last modified time | relevance | path

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

12345678910>>...14

/linux/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/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 …]
H A Dcrct10dif-ce-core.S275 CPU_LE( rev64 v0.16b, v0.16b )
283 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
295 eor v0.16b, v0.16b, v8.16b
346 CPU_LE( rev64 v0.16b, v0.16b )
347 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
368 CPU_LE( rev64 v0.16b, v0.16b )
369 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
409 eor v0.16b, v0.16b, v7.16b // + low bits * x^64
416 eor v0.16b, v0.16b, v1.16b // + low bits
426 ushr v0.2d, v0.2d, #48
[all …]
/linux/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/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/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/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/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/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/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/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/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 …]
/linux/drivers/gpu/drm/amd/amdkfd/
H A Dcwsr_trap_handler_gfx10.asm840 v_mbcnt_hi_u32_b32 v0, -1, v0
841 v_mul_u32_u24 v0, 4, v0
962 v_movrels_b32 v0, v0 //v0 = v[0+m0]
977 v_movrels_b32 v0, v0 //v0 = v[0+m0]
1007 v_movrels_b32 v0, v0 //v0 = v[0+m0]
1022 v_movrels_b32 v0, v0 //v0 = v[0+m0]
1054 v_movrels_b32 v0, v0
1066 v_movrels_b32 v0, v0 //v0 = v[0+m0]
1194 v_movreld_b32 v0, v0 //v[0+m0] = v0
1228 v_movreld_b32 v0, v0 //v[0+m0] = v0
[all …]
/linux/arch/powerpc/crypto/
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/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/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/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 …]
/linux/tools/testing/selftests/bpf/
H A Dtest_xdp_features.sh16 ip link add v1 type veth peer name v0 netns ${NS}
21 ip -n ${NS} link set dev v0 up
22 ip -n ${NS} addr add $V0_IP4/24 dev v0
23 ip -n ${NS} addr add $V0_IP6/64 nodad dev v0
28 ip netns exec ${NS} ethtool -K v0 gro on
54 -T $V0_IP6 v0
63 -T ::ffff:$V0_IP4 v0
71 -T $V0_IP6 v0
80 -T ::ffff:$V0_IP4 v0
88 -T $V0_IP6 v0
[all …]

12345678910>>...14