Home
last modified time | relevance | path

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

12345678910>>...17

/OK3568_Linux_fs/kernel/drivers/gpu/drm/nouveau/nvkm/core/
H A Dioctl.c36 struct nvif_ioctl_nop_v0 v0; in nvkm_ioctl_nop() member
41 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_ioctl_nop()
42 nvif_ioctl(object, "nop vers %lld\n", args->v0.version); in nvkm_ioctl_nop()
43 args->v0.version = NVIF_VERSION_LATEST; in nvkm_ioctl_nop()
54 struct nvif_ioctl_sclass_v0 v0; in nvkm_ioctl_sclass() member
60 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) { in nvkm_ioctl_sclass()
62 args->v0.version, args->v0.count); in nvkm_ioctl_sclass()
63 if (size != args->v0.count * sizeof(args->v0.oclass[0])) in nvkm_ioctl_sclass()
68 if (i < args->v0.count) { in nvkm_ioctl_sclass()
69 args->v0.oclass[i].oclass = oclass.base.oclass; in nvkm_ioctl_sclass()
[all …]
H A Dclient.c39 struct nvif_client_v0 v0; in nvkm_uclient_new() member
44 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, false))){ in nvkm_uclient_new()
45 args->v0.name[sizeof(args->v0.name) - 1] = 0; in nvkm_uclient_new()
46 ret = nvkm_client_new(args->v0.name, args->v0.device, NULL, in nvkm_uclient_new()
77 struct nvif_notify_rep_v0 v0; member
134 struct nvif_notify_req_v0 v0; in nvkm_client_notify_new() member
152 if (!(ret = nvif_unpack(ret, &data, &size, req->v0, 0, 0, true))) { in nvkm_client_notify_new()
154 "token %llx\n", req->v0.version, in nvkm_client_notify_new()
155 req->v0.reply, req->v0.route, req->v0.token); in nvkm_client_notify_new()
156 notify->version = req->v0.version; in nvkm_client_notify_new()
[all …]
/OK3568_Linux_fs/kernel/drivers/gpu/drm/nouveau/nvkm/engine/disp/
H A Drootnv50.c40 struct nv50_disp_mthd_v0 v0; in nv50_disp_root_mthd_() member
54 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) { in nv50_disp_root_mthd_()
56 args->v0.version, args->v0.method, args->v0.head); in nv50_disp_root_mthd_()
57 mthd = args->v0.method; in nv50_disp_root_mthd_()
58 hidx = args->v0.head; in nv50_disp_root_mthd_()
98 struct nv50_disp_acquire_v0 v0; in nv50_disp_root_mthd_() member
101 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nv50_disp_root_mthd_()
102 ret = nvkm_outp_acquire(outp, NVKM_OUTP_USER, args->v0.hda); in nv50_disp_root_mthd_()
104 args->v0.or = outp->ior->id; in nv50_disp_root_mthd_()
105 args->v0.link = outp->ior->asy.link; in nv50_disp_root_mthd_()
[all …]
H A Dhead.c47 struct nv04_disp_scanoutpos_v0 v0; in nvkm_head_mthd_scanoutpos() member
52 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_head_mthd_scanoutpos()
54 args->v0.version); in nvkm_head_mthd_scanoutpos()
57 args->v0.vtotal = head->arm.vtotal; in nvkm_head_mthd_scanoutpos()
58 args->v0.vblanks = head->arm.vblanks; in nvkm_head_mthd_scanoutpos()
59 args->v0.vblanke = head->arm.vblanke; in nvkm_head_mthd_scanoutpos()
60 args->v0.htotal = head->arm.htotal; in nvkm_head_mthd_scanoutpos()
61 args->v0.hblanks = head->arm.hblanks; in nvkm_head_mthd_scanoutpos()
62 args->v0.hblanke = head->arm.hblanke; in nvkm_head_mthd_scanoutpos()
68 if (!args->v0.vtotal || !args->v0.htotal) in nvkm_head_mthd_scanoutpos()
[all …]
/OK3568_Linux_fs/kernel/arch/arm64/crypto/
H A Daes-ce-ccm-core.S20 ld1 {v0.16b}, [x0] /* load mac */
31 eor v0.16b, v0.16b, v1.16b
43 3: aese v0.16b, v4.16b
44 aesmc v0.16b, v0.16b
46 aese v0.16b, v5.16b
47 aesmc v0.16b, v0.16b
50 aese v0.16b, v3.16b
51 aesmc v0.16b, v0.16b
54 aese v0.16b, v4.16b
56 eor v0.16b, v0.16b, v5.16b /* final round */
[all …]
H A Daes-ce-core.S13 ld1 {v0.16b}, [x2]
22 1: aese v0.16b, v2.16b
23 aesmc v0.16b, v0.16b
25 aese v0.16b, v3.16b
26 aesmc v0.16b, v0.16b
29 aese v0.16b, v1.16b
30 aesmc v0.16b, v0.16b
33 aese v0.16b, v2.16b
34 eor v0.16b, v0.16b, v3.16b
35 st1 {v0.16b}, [x1]
[all …]
H A Daes-modes.S26 encrypt_block4x v0, v1, v2, v3, w3, x2, x8, w7
31 decrypt_block4x v0, v1, v2, v3, w3, x2, x8, w7
37 encrypt_block5x v0, v1, v2, v3, v4, w3, x2, x8, w7
42 decrypt_block5x v0, v1, v2, v3, v4, w3, x2, x8, w7
63 ld1 {v0.16b-v3.16b}, [x1], #64 /* get 4 pt blocks */
67 st1 {v0.16b-v3.16b}, [x0], #64
74 ld1 {v0.16b}, [x1], #16 /* get next pt block */
75 encrypt_block v0, w3, x2, x5, w6
76 st1 {v0.16b}, [x0], #16
94 ld1 {v0.16b-v3.16b}, [x1], #64 /* get 4 ct blocks */
[all …]
/OK3568_Linux_fs/kernel/drivers/gpu/drm/nouveau/nvkm/engine/device/
H A Dctrl.c38 struct nvif_control_pstate_info_v0 v0; in nvkm_control_mthd_pstate_info() member
44 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_control_mthd_pstate_info()
46 args->v0.version); in nvkm_control_mthd_pstate_info()
51 args->v0.count = clk->state_nr; in nvkm_control_mthd_pstate_info()
52 args->v0.ustate_ac = clk->ustate_ac; in nvkm_control_mthd_pstate_info()
53 args->v0.ustate_dc = clk->ustate_dc; in nvkm_control_mthd_pstate_info()
54 args->v0.pwrsrc = clk->pwrsrc; in nvkm_control_mthd_pstate_info()
55 args->v0.pstate = clk->pstate; in nvkm_control_mthd_pstate_info()
57 args->v0.count = 0; in nvkm_control_mthd_pstate_info()
58 args->v0.ustate_ac = NVIF_CONTROL_PSTATE_INFO_V0_USTATE_DISABLE; in nvkm_control_mthd_pstate_info()
[all …]
H A Duser.c110 struct nv_device_info_v0 v0; in nvkm_udevice_info() member
126 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_udevice_info()
127 nvif_ioctl(object, "device info vers %d\n", args->v0.version); in nvkm_udevice_info()
142 args->v0.platform = NV_DEVICE_INFO_V0_IGP; in nvkm_udevice_info()
147 args->v0.platform = NV_DEVICE_INFO_V0_PCI; in nvkm_udevice_info()
150 args->v0.platform = NV_DEVICE_INFO_V0_AGP; in nvkm_udevice_info()
153 args->v0.platform = NV_DEVICE_INFO_V0_PCIE; in nvkm_udevice_info()
156 args->v0.platform = NV_DEVICE_INFO_V0_SOC; in nvkm_udevice_info()
166 case NV_04: args->v0.family = NV_DEVICE_INFO_V0_TNT; break; in nvkm_udevice_info()
168 case NV_11: args->v0.family = NV_DEVICE_INFO_V0_CELSIUS; break; in nvkm_udevice_info()
[all …]
/OK3568_Linux_fs/kernel/drivers/gpu/drm/nouveau/
H A Dnouveau_usif.c77 struct nvif_notify_rep_v0 v0; in usif_notify() member
83 if (length == sizeof(rep->v0) && rep->v0.version == 0) { in usif_notify()
84 if (WARN_ON(!(ntfy = (void *)(unsigned long)rep->v0.token))) in usif_notify()
86 BUG_ON(rep->v0.route != NVDRM_NOTIFY_USIF); in usif_notify()
98 switch (rep->v0.version) { in usif_notify()
127 struct nvif_ioctl_ntfy_new_v0 v0; in usif_notify_new() member
130 struct nvif_notify_req_v0 v0; in usif_notify_new() member
135 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) { in usif_notify_new()
136 if (usif_notify_find(f, args->v0.index)) in usif_notify_new()
147 if (!(ret = nvif_unpack(ret, &data, &size, req->v0, 0, 0, true))) { in usif_notify_new()
[all …]
/OK3568_Linux_fs/kernel/drivers/media/platform/rockchip/isp/
H A Dprocfs.c381 u32 v0, v1; in isp30_unite_show() local
383 v0 = rkisp_read(dev, ISP3X_CMSK_CTRL0, false); in isp30_unite_show()
387 (v0 & 1) ? "ON" : "OFF", in isp30_unite_show()
388 v0, (v1 & 1) ? "ON" : "OFF", v1); in isp30_unite_show()
389 v0 = rkisp_read(dev, ISP3X_DPCC0_MODE, false); in isp30_unite_show()
393 (v0 & 1) ? "ON" : "OFF", v0, in isp30_unite_show()
395 v0 = rkisp_read(dev, ISP3X_DPCC1_MODE, false); in isp30_unite_show()
399 (v0 & 1) ? "ON" : "OFF", v0, in isp30_unite_show()
401 v0 = rkisp_read(dev, ISP3X_DPCC2_MODE, false); in isp30_unite_show()
405 (v0 & 1) ? "ON" : "OFF", v0, in isp30_unite_show()
[all …]
/OK3568_Linux_fs/kernel/drivers/gpu/drm/nouveau/nvkm/subdev/mmu/
H A Dummu.c61 struct nvif_mmu_heap_v0 v0; in nvkm_ummu_heap() member
66 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, false))) { in nvkm_ummu_heap()
67 if ((index = args->v0.index) >= mmu->heap_nr) in nvkm_ummu_heap()
69 args->v0.size = mmu->heap[index].size; in nvkm_ummu_heap()
81 struct nvif_mmu_type_v0 v0; in nvkm_ummu_type() member
86 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, false))) { in nvkm_ummu_type()
87 if ((index = args->v0.index) >= mmu->type_nr) in nvkm_ummu_type()
90 args->v0.heap = mmu->type[index].heap; in nvkm_ummu_type()
91 args->v0.vram = !!(type & NVKM_MEM_VRAM); in nvkm_ummu_type()
92 args->v0.host = !!(type & NVKM_MEM_HOST); in nvkm_ummu_type()
[all …]
H A Duvmm.c50 struct nvif_vmm_pfnclr_v0 v0; in nvkm_uvmm_mthd_pfnclr() member
56 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, false))) { in nvkm_uvmm_mthd_pfnclr()
57 addr = args->v0.addr; in nvkm_uvmm_mthd_pfnclr()
58 size = args->v0.size; in nvkm_uvmm_mthd_pfnclr()
79 struct nvif_vmm_pfnmap_v0 v0; in nvkm_uvmm_mthd_pfnmap() member
86 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, true))) { in nvkm_uvmm_mthd_pfnmap()
87 page = args->v0.page; in nvkm_uvmm_mthd_pfnmap()
88 addr = args->v0.addr; in nvkm_uvmm_mthd_pfnmap()
89 size = args->v0.size; in nvkm_uvmm_mthd_pfnmap()
90 phys = args->v0.phys; in nvkm_uvmm_mthd_pfnmap()
[all …]
/OK3568_Linux_fs/kernel/arch/mips/include/asm/mach-cavium-octeon/
H A Dkernel-entry-init.h30 dmfc0 v0, CP0_CVMMEMCTL_REG
32 dins v0, $0, 0, 6
33 ori v0, CONFIG_CAVIUM_OCTEON_CVMSEG_SIZE
34 dmtc0 v0, CP0_CVMMEMCTL_REG # Write the cavium mem control register
35 dmfc0 v0, CP0_CVMCTL_REG # Read the cavium control register
38 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.
[all …]
/OK3568_Linux_fs/kernel/drivers/gpu/drm/nouveau/nvkm/engine/fifo/
H A Dgpfifotu102.c57 struct volta_channel_gpfifo_a_v0 v0; in tu102_fifo_gpfifo_new() member
62 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in tu102_fifo_gpfifo_new()
66 args->v0.version, args->v0.vmm, args->v0.ioffset, in tu102_fifo_gpfifo_new()
67 args->v0.ilength, args->v0.runlist, args->v0.priv); in tu102_fifo_gpfifo_new()
68 if (args->v0.priv && !oclass->client->super) in tu102_fifo_gpfifo_new()
71 &args->v0.runlist, in tu102_fifo_gpfifo_new()
72 &args->v0.chid, in tu102_fifo_gpfifo_new()
73 args->v0.vmm, in tu102_fifo_gpfifo_new()
74 args->v0.ioffset, in tu102_fifo_gpfifo_new()
75 args->v0.ilength, in tu102_fifo_gpfifo_new()
[all …]
H A Ddmanv50.c39 struct nv50_channel_dma_v0 v0; in nv50_fifo_dma_new() member
46 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nv50_fifo_dma_new()
49 args->v0.version, args->v0.vmm, args->v0.pushbuf, in nv50_fifo_dma_new()
50 args->v0.offset); in nv50_fifo_dma_new()
51 if (!args->v0.pushbuf) in nv50_fifo_dma_new()
60 ret = nv50_fifo_chan_ctor(fifo, args->v0.vmm, args->v0.pushbuf, in nv50_fifo_dma_new()
65 args->v0.chid = chan->base.chid; in nv50_fifo_dma_new()
68 nvkm_wo32(chan->ramfc, 0x08, lower_32_bits(args->v0.offset)); in nv50_fifo_dma_new()
69 nvkm_wo32(chan->ramfc, 0x0c, upper_32_bits(args->v0.offset)); in nv50_fifo_dma_new()
70 nvkm_wo32(chan->ramfc, 0x10, lower_32_bits(args->v0.offset)); in nv50_fifo_dma_new()
[all …]
H A Ddmag84.c39 struct g82_channel_dma_v0 v0; in g84_fifo_dma_new() member
46 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in g84_fifo_dma_new()
49 args->v0.version, args->v0.vmm, args->v0.pushbuf, in g84_fifo_dma_new()
50 args->v0.offset); in g84_fifo_dma_new()
51 if (!args->v0.pushbuf) in g84_fifo_dma_new()
60 ret = g84_fifo_chan_ctor(fifo, args->v0.vmm, args->v0.pushbuf, in g84_fifo_dma_new()
65 args->v0.chid = chan->base.chid; in g84_fifo_dma_new()
68 nvkm_wo32(chan->ramfc, 0x08, lower_32_bits(args->v0.offset)); in g84_fifo_dma_new()
69 nvkm_wo32(chan->ramfc, 0x0c, upper_32_bits(args->v0.offset)); in g84_fifo_dma_new()
70 nvkm_wo32(chan->ramfc, 0x10, lower_32_bits(args->v0.offset)); in g84_fifo_dma_new()
[all …]
H A Dgpfifonv50.c39 struct nv50_channel_gpfifo_v0 v0; in nv50_fifo_gpfifo_new() member
47 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nv50_fifo_gpfifo_new()
51 args->v0.version, args->v0.vmm, args->v0.pushbuf, in nv50_fifo_gpfifo_new()
52 args->v0.ioffset, args->v0.ilength); in nv50_fifo_gpfifo_new()
53 if (!args->v0.pushbuf) in nv50_fifo_gpfifo_new()
62 ret = nv50_fifo_chan_ctor(fifo, args->v0.vmm, args->v0.pushbuf, in nv50_fifo_gpfifo_new()
67 args->v0.chid = chan->base.chid; in nv50_fifo_gpfifo_new()
68 ioffset = args->v0.ioffset; in nv50_fifo_gpfifo_new()
69 ilength = order_base_2(args->v0.ilength / 8); in nv50_fifo_gpfifo_new()
/OK3568_Linux_fs/kernel/lib/
H A Dsiphash.c21 #define SIPROUND SIPHASH_PERMUTATION(v0, v1, v2, v3)
24 u64 v0 = SIPHASH_CONST_0; \
32 v0 ^= key->key[0];
38 v0 ^= b; \
44 return (v0 ^ v1) ^ (v2 ^ v3);
58 v0 ^= m; in __siphash_aligned()
91 v0 ^= m; in __siphash_unaligned()
123 v0 ^= first; in siphash_1u64()
140 v0 ^= first; in siphash_2u64()
144 v0 ^= second; in siphash_2u64()
[all …]
H A Drandom32.c335 unsigned long v0; member
366 unsigned long v0 = s->v0, v1 = s->v1, v2 = s->v2, v3 = s->v3; in siprand_u32() local
370 PRND_SIPROUND(v0, v1, v2, v3); in siprand_u32()
371 PRND_SIPROUND(v0, v1, v2, v3); in siprand_u32()
372 v0 ^= n; in siprand_u32()
373 s->v0 = v0; s->v1 = v1; s->v2 = v2; s->v3 = v3; in siprand_u32()
440 unsigned long v0 = state->v0, v1 = state->v1; in prandom_seed() local
445 PRND_SIPROUND(v0, v1, v2, v3); in prandom_seed()
446 PRND_SIPROUND(v0, v1, v2, v3); in prandom_seed()
447 v0 ^= entropy; in prandom_seed()
[all …]
/OK3568_Linux_fs/kernel/tools/testing/selftests/powerpc/math/
H A Dvmx_asm.S9 # Should be safe from C, only touches r4, r5 and v0,v1,v2
15 lvx v0,r5,r4
16 vcmpequd. v1,v0,v20
20 lvx v0,r5,r4
21 vcmpequd. v1,v0,v21
25 lvx v0,r5,r4
26 vcmpequd. v1,v0,v22
30 lvx v0,r5,r4
31 vcmpequd. v1,v0,v23
35 lvx v0,r5,r4
[all …]
/OK3568_Linux_fs/kernel/arch/arm64/lib/
H A Dxor-neon.c19 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_2() local
24 v0 = veorq_u64(vld1q_u64(dp1 + 0), vld1q_u64(dp2 + 0)); in xor_arm64_neon_2()
30 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_2()
47 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
52 v0 = veorq_u64(vld1q_u64(dp1 + 0), vld1q_u64(dp2 + 0)); in xor_arm64_neon_3()
58 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_3()
64 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_3()
83 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
88 v0 = veorq_u64(vld1q_u64(dp1 + 0), vld1q_u64(dp2 + 0)); in xor_arm64_neon_4()
94 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_4()
[all …]
/OK3568_Linux_fs/kernel/drivers/gpu/drm/nouveau/nvkm/engine/pm/
H A Dbase.c265 struct nvif_perfdom_read_v0 v0; in nvkm_perfdom_read() member
272 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_perfdom_read()
273 nvif_ioctl(object, "perfdom read vers %d\n", args->v0.version); in nvkm_perfdom_read()
287 args->v0.ctr[i] = dom->ctr[i]->ctr; in nvkm_perfdom_read()
288 args->v0.clk = dom->clk; in nvkm_perfdom_read()
371 struct nvif_perfdom_v0 v0; in nvkm_perfdom_new_() member
382 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_perfdom_new_()
384 args->v0.version, args->v0.domain, args->v0.mode); in nvkm_perfdom_new_()
388 for (c = 0; c < ARRAY_SIZE(args->v0.ctr); c++) { in nvkm_perfdom_new_()
392 for (s = 0; s < ARRAY_SIZE(args->v0.ctr[c].signal); s++) { in nvkm_perfdom_new_()
[all …]
/OK3568_Linux_fs/kernel/arch/powerpc/crypto/
H A Dcrc32-vpmsum_core.S101 vspltisw v0,-1
103 vsldoi mask_32bit,zeroes,v0,4
104 vsldoi mask_64bit,zeroes,v0,8
160 vxor v0,v0,v0
259 vxor v0,v0,v8
316 vxor v0,v0,v8
350 vxor v0,v0,v8
366 vsldoi v0,v0,zeroes,4
396 vxor v16,v0,v8
425 lvx v0,0,r3
[all …]
/OK3568_Linux_fs/kernel/drivers/gpu/drm/amd/amdkfd/
H A Dcwsr_trap_handler_gfx10.asm364 buffer_store_dword v0, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1
365 buffer_store_dword v1, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1 offset:128
366 buffer_store_dword v2, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1 offset:128*2
367 buffer_store_dword v3, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1 offset:128*3
375 buffer_store_dword v0, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1
376 buffer_store_dword v1, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1 offset:256
377 buffer_store_dword v2, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1 offset:256*2
378 buffer_store_dword v3, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1 offset:256*3
392 v_mov_b32 v0, 0x0 //Offset[31:0] from buffer resource
423 buffer_store_dword v2, v0, s_save_buf_rsrc0, s_save_mem_offset slc:1 glc:1
[all …]

12345678910>>...17