| /linux-6.1.9/drivers/gpu/drm/nouveau/nvkm/core/ |
| D | ioctl.c | 37 struct nvif_ioctl_nop_v0 v0; in nvkm_ioctl_nop() member
42 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_ioctl_nop()
43 nvif_ioctl(object, "nop vers %lld\n", args->v0.version); in nvkm_ioctl_nop()
44 args->v0.version = NVIF_VERSION_LATEST; in nvkm_ioctl_nop()
55 struct nvif_ioctl_sclass_v0 v0; in nvkm_ioctl_sclass() member
61 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) { in nvkm_ioctl_sclass()
63 args->v0.version, args->v0.count); in nvkm_ioctl_sclass()
64 if (size != args->v0.count * sizeof(args->v0.oclass[0])) in nvkm_ioctl_sclass()
69 if (i < args->v0.count) { in nvkm_ioctl_sclass()
70 args->v0.oclass[i].oclass = oclass.base.oclass; in nvkm_ioctl_sclass()
[all …]
|
| D | client.c | 39 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 …]
|
| /linux-6.1.9/drivers/gpu/drm/nouveau/nvkm/engine/disp/ |
| D | rootnv50.c | 39 struct nv50_disp_mthd_v0 v0; in nv50_disp_root_mthd_() member
52 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) { in nv50_disp_root_mthd_()
54 args->v0.version, args->v0.method, args->v0.head); in nv50_disp_root_mthd_()
55 mthd = args->v0.method; in nv50_disp_root_mthd_()
56 hidx = args->v0.head; in nv50_disp_root_mthd_()
96 struct nv50_disp_acquire_v0 v0; in nv50_disp_root_mthd_() member
99 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nv50_disp_root_mthd_()
100 ret = nvkm_outp_acquire(outp, NVKM_OUTP_USER, args->v0.hda); in nv50_disp_root_mthd_()
102 args->v0.or = outp->ior->id; in nv50_disp_root_mthd_()
103 args->v0.link = outp->ior->asy.link; in nv50_disp_root_mthd_()
[all …]
|
| D | head.c | 47 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 …]
|
| /linux-6.1.9/arch/arm64/crypto/ |
| D | aes-ce-core.S | 13 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 …]
|
| D | aes-ce-ccm-core.S | 19 ld1 {v0.16b}, [x0] /* load mac */
30 eor v0.16b, v0.16b, v1.16b
42 3: aese v0.16b, v4.16b
43 aesmc v0.16b, v0.16b
45 aese v0.16b, v5.16b
46 aesmc v0.16b, v0.16b
49 aese v0.16b, v3.16b
50 aesmc v0.16b, v0.16b
53 aese v0.16b, v4.16b
55 eor v0.16b, v0.16b, v5.16b /* final round */
[all …]
|
| D | aes-modes.S | 26 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 …]
|
| D | sm4-ce-core.S | 215 ld1 {v0.16b}, [x0];
216 rev32 v0.16b, v0.16b;
223 eor v0.16b, v0.16b, v1.16b;
225 sm4ekey v0.4s, v0.4s, v24.4s;
226 sm4ekey v1.4s, v0.4s, v25.4s;
234 st1 {v0.16b-v3.16b}, [x1], #64;
243 rev64 v0.4s, v0.4s;
251 ext v0.16b, v0.16b, v0.16b, #8;
259 st1 {v0.16b}, [x2];
273 ld1 {v0.16b}, [x2];
[all …]
|
| /linux-6.1.9/drivers/gpu/drm/nouveau/nvkm/engine/device/ |
| D | ctrl.c | 38 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 …]
|
| D | user.c | 80 struct nv_device_info_v0 v0; in nvkm_udevice_info() member
96 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in nvkm_udevice_info()
97 nvif_ioctl(object, "device info vers %d\n", args->v0.version); in nvkm_udevice_info()
112 args->v0.platform = NV_DEVICE_INFO_V0_IGP; in nvkm_udevice_info()
117 args->v0.platform = NV_DEVICE_INFO_V0_PCI; in nvkm_udevice_info()
120 args->v0.platform = NV_DEVICE_INFO_V0_AGP; in nvkm_udevice_info()
123 args->v0.platform = NV_DEVICE_INFO_V0_PCIE; in nvkm_udevice_info()
126 args->v0.platform = NV_DEVICE_INFO_V0_SOC; in nvkm_udevice_info()
136 case NV_04: args->v0.family = NV_DEVICE_INFO_V0_TNT; break; in nvkm_udevice_info()
138 case NV_11: args->v0.family = NV_DEVICE_INFO_V0_CELSIUS; break; in nvkm_udevice_info()
[all …]
|
| /linux-6.1.9/drivers/gpu/drm/nouveau/ |
| D | nouveau_usif.c | 55 struct nvif_ioctl_new_v0 v0; in usif_object_new() member
60 if ((ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) in usif_object_new()
63 switch (args->v0.oclass) { in usif_object_new()
70 struct nv_device_v0 v0; in usif_object_new() member
73 if ((ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) in usif_object_new()
76 args->v0.priv = false; in usif_object_new()
89 object->route = args->v0.route; in usif_object_new()
90 object->token = args->v0.token; in usif_object_new()
91 args->v0.route = NVDRM_OBJECT_USIF; in usif_object_new()
92 args->v0.token = (unsigned long)(void *)object; in usif_object_new()
[all …]
|
| /linux-6.1.9/drivers/gpu/drm/nouveau/nvkm/subdev/mmu/ |
| D | ummu.c | 61 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 …]
|
| D | uvmm.c | 49 struct nvif_vmm_pfnclr_v0 v0; in nvkm_uvmm_mthd_pfnclr() member
55 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, false))) { in nvkm_uvmm_mthd_pfnclr()
56 addr = args->v0.addr; in nvkm_uvmm_mthd_pfnclr()
57 size = args->v0.size; in nvkm_uvmm_mthd_pfnclr()
74 struct nvif_vmm_pfnmap_v0 v0; in nvkm_uvmm_mthd_pfnmap() member
81 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, true))) { in nvkm_uvmm_mthd_pfnmap()
82 page = args->v0.page; in nvkm_uvmm_mthd_pfnmap()
83 addr = args->v0.addr; in nvkm_uvmm_mthd_pfnmap()
84 size = args->v0.size; in nvkm_uvmm_mthd_pfnmap()
85 phys = args->v0.phys; in nvkm_uvmm_mthd_pfnmap()
[all …]
|
| /linux-6.1.9/drivers/gpu/drm/nouveau/nvkm/engine/fifo/ |
| D | gpfifotu102.c | 57 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()
69 &args->v0.runlist, in tu102_fifo_gpfifo_new()
70 &args->v0.chid, in tu102_fifo_gpfifo_new()
71 args->v0.vmm, in tu102_fifo_gpfifo_new()
72 args->v0.ioffset, in tu102_fifo_gpfifo_new()
73 args->v0.ilength, in tu102_fifo_gpfifo_new()
74 &args->v0.inst, in tu102_fifo_gpfifo_new()
[all …]
|
| D | gpfifonv50.c | 39 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()
|
| D | gpfifog84.c | 39 struct g82_channel_gpfifo_v0 v0; in g84_fifo_gpfifo_new() member
47 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, false))) { in g84_fifo_gpfifo_new()
51 args->v0.version, args->v0.vmm, args->v0.pushbuf, in g84_fifo_gpfifo_new()
52 args->v0.ioffset, args->v0.ilength); in g84_fifo_gpfifo_new()
53 if (!args->v0.pushbuf) in g84_fifo_gpfifo_new()
62 ret = g84_fifo_chan_ctor(fifo, args->v0.vmm, args->v0.pushbuf, in g84_fifo_gpfifo_new()
67 args->v0.chid = chan->base.chid; in g84_fifo_gpfifo_new()
68 ioffset = args->v0.ioffset; in g84_fifo_gpfifo_new()
69 ilength = order_base_2(args->v0.ilength / 8); in g84_fifo_gpfifo_new()
|
| /linux-6.1.9/arch/mips/include/asm/mach-cavium-octeon/ |
| D | kernel-entry-init.h | 30 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 …]
|
| /linux-6.1.9/tools/testing/selftests/powerpc/math/ |
| D | vmx_asm.S | 9 # 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 …]
|
| /linux-6.1.9/lib/ |
| D | siphash.c | 20 #define SIPROUND SIPHASH_PERMUTATION(v0, v1, v2, v3)
23 u64 v0 = SIPHASH_CONST_0; \
31 v0 ^= key->key[0];
37 v0 ^= b; \
43 return (v0 ^ v1) ^ (v2 ^ v3);
57 v0 ^= m; in __siphash_aligned()
90 v0 ^= m; in __siphash_unaligned()
122 v0 ^= first; in siphash_1u64()
139 v0 ^= first; in siphash_2u64()
143 v0 ^= second; in siphash_2u64()
[all …]
|
| D | atomic64_test.c | 22 atomic##bit##_set(&v, v0); \
23 r = v0; \
46 atomic##bit##_set(&v, v0); \
47 r = v0; \
55 atomic##bit##_set(&v, v0); \
56 r = v0; \
58 BUG_ON(atomic##bit##_##op(val, &v) != v0); \
106 int v0 = 0xaaa31337; in test_atomic() local
138 INC_RETURN_FAMILY_TEST(, v0); in test_atomic()
139 DEC_RETURN_FAMILY_TEST(, v0); in test_atomic()
[all …]
|
| /linux-6.1.9/arch/arm64/lib/ |
| D | xor-neon.c | 19 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()
48 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_3() local
53 v0 = veorq_u64(vld1q_u64(dp1 + 0), vld1q_u64(dp2 + 0)); in xor_arm64_neon_3()
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()
86 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_4() local
91 v0 = veorq_u64(vld1q_u64(dp1 + 0), vld1q_u64(dp2 + 0)); in xor_arm64_neon_4()
97 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_4()
[all …]
|
| /linux-6.1.9/drivers/gpu/drm/amd/amdkfd/ |
| D | cwsr_trap_handler_gfx10.asm | 374 global_store_dword_addtid v0, [s_save_ttmps_lo, s_save_ttmps_hi] slc:1 glc:1
375 v_mov_b32 v0, 0x0
392 v_writelane_b32 v0, ttmp4, 0x4
393 v_writelane_b32 v0, ttmp5, 0x5
394 v_writelane_b32 v0, ttmp6, 0x6
395 v_writelane_b32 v0, ttmp7, 0x7
396 v_writelane_b32 v0, ttmp8, 0x8
397 v_writelane_b32 v0, ttmp9, 0x9
398 v_writelane_b32 v0, ttmp10, 0xA
399 v_writelane_b32 v0, ttmp11, 0xB
[all …]
|
| /linux-6.1.9/drivers/gpu/drm/nouveau/nvkm/engine/pm/ |
| D | base.c | 265 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 …]
|
| /linux-6.1.9/arch/powerpc/crypto/ |
| D | crc32-vpmsum_core.S | 101 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 …]
|
| /linux-6.1.9/arch/mips/lib/ |
| D | strncpy_user.S | 38 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
|