| /linux/drivers/gpu/drm/nouveau/nvkm/engine/disp/ |
| H A D | uoutp.c | 38 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 D | uconn.c | 38 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 D | uhead.c | 50 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/drivers/gpu/drm/nouveau/nvkm/core/ |
| H A D | ioctl.c | 83 args->v0.version, args->v0.count); in nvkm_ioctl_sclass()
84 if (size != args->v0.count * sizeof(args->v0.oclass[0])) in nvkm_ioctl_sclass()
96 args->v0.count = i; in nvkm_ioctl_sclass()
117 args->v0.version, args->v0.handle, args->v0.oclass, in nvkm_ioctl_new()
118 args->v0.route, args->v0.token, args->v0.object); in nvkm_ioctl_new()
196 args->v0.version, args->v0.method); in nvkm_ioctl_mthd()
221 args->v0.version, args->v0.size, args->v0.addr); in nvkm_ioctl_rd()
257 args->v0.version, args->v0.size, args->v0.addr, in nvkm_ioctl_wr()
374 args->v0.version, args->v0.type, args->v0.object, in nvkm_ioctl()
376 ret = nvkm_ioctl_path(client, args->v0.object, args->v0.type, in nvkm_ioctl()
[all …]
|
| H A D | client.c | 38 struct nvif_client_v0 v0; in nvkm_uclient_new() member
43 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, false))){ in nvkm_uclient_new()
44 args->v0.name[sizeof(args->v0.name) - 1] = 0; in nvkm_uclient_new()
45 ret = nvkm_client_new(args->v0.name, args->v0.device, NULL, in nvkm_uclient_new()
87 struct nvif_client_devlist_v0 v0; in nvkm_client_mthd_devlist() member
92 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) { in nvkm_client_mthd_devlist()
94 args->v0.version, args->v0.count); in nvkm_client_mthd_devlist()
95 if (size == sizeof(args->v0.device[0]) * args->v0.count) { in nvkm_client_mthd_devlist()
96 ret = nvkm_device_list(args->v0.device, args->v0.count); in nvkm_client_mthd_devlist()
98 args->v0.count = ret; in nvkm_client_mthd_devlist()
|
| /linux/arch/arm64/crypto/ |
| H A D | aes-ce-core.S | 13 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 D | sm4-ce-core.S | 52 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 D | aes-modes.S | 196 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/drivers/gpu/drm/nouveau/nvkm/engine/device/ |
| H A D | ctrl.c | 46 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 D | user.c | 80 struct nv_device_info_v0 v0; in nvkm_udevice_info() member
152 args->v0.family = 0; 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()
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()
388 struct nv_device_v0 v0; in nvkm_udevice_new() member
399 args->v0.version, args->v0.device); in nvkm_udevice_new()
404 if (args->v0.priv) in nvkm_udevice_new()
[all …]
|
| /linux/drivers/gpu/drm/nouveau/ |
| H A D | nouveau_usif.c | 55 struct nvif_ioctl_new_v0 v0; in usif_object_new() member
63 switch (args->v0.oclass) { in usif_object_new()
70 struct nv_device_v0 v0; in usif_object_new() member
76 args->v0.priv = false; in usif_object_new()
89 object->route = args->v0.route; in usif_object_new()
112 struct nvif_ioctl_v0 v0; in usif_ioctl() member
126 owner = argv->v0.owner; in usif_ioctl()
139 if (argv->v0.route) { in usif_ioctl()
150 switch (argv->v0.type) { in usif_ioctl()
168 argv->v0.token = 0; in usif_ioctl()
[all …]
|
| /linux/drivers/gpu/drm/nouveau/nvkm/subdev/mmu/ |
| H A D | ummu.c | 61 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 D | uvmm.c | 56 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/arch/mips/include/asm/mach-cavium-octeon/ |
| H A D | kernel-entry-init.h | 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.
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 D | xor.S | 11 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/drivers/gpu/drm/amd/amdkfd/ |
| H A D | cwsr_trap_handler_gfx10.asm | 675 v_mbcnt_hi_u32_b32 v0, -1, v0
676 v_mul_u32_u24 v0, 4, v0
797 v_movrels_b32 v0, v0 //v0 = v[0+m0]
812 v_movrels_b32 v0, v0 //v0 = v[0+m0]
842 v_movrels_b32 v0, v0 //v0 = v[0+m0]
857 v_movrels_b32 v0, v0 //v0 = v[0+m0]
889 v_movrels_b32 v0, v0
901 v_movrels_b32 v0, v0 //v0 = v[0+m0]
1025 v_movreld_b32 v0, v0 //v[0+m0] = v0
1059 v_movreld_b32 v0, v0 //v[0+m0] = v0
[all …]
|
| /linux/tools/testing/selftests/powerpc/math/ |
| H A D | vmx_asm.S | 15 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 D | if0012.h | 41 } 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 D | siphash.c | 37 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 D | atomic64_test.c | 22 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 D | xor-neon.c | 30 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/nouveau/nvkm/engine/pm/ |
| H A D | base.c | 384 args->v0.version, args->v0.domain, args->v0.mode); in nvkm_perfdom_new_()
449 args->v0.version, args->v0.iter); in nvkm_perfmon_mthd_query_domain()
465 strscpy(args->v0.name, dom->name, sizeof(args->v0.name)); in nvkm_perfmon_mthd_query_domain()
477 args->v0.iter = 0xff; in nvkm_perfmon_mthd_query_domain()
501 args->v0.version, args->v0.domain, args->v0.iter); in nvkm_perfmon_mthd_query_signal()
513 snprintf(args->v0.name, sizeof(args->v0.name), in nvkm_perfmon_mthd_query_signal()
516 strscpy(args->v0.name, sig->name, sizeof(args->v0.name)); in nvkm_perfmon_mthd_query_signal()
553 args->v0.version, args->v0.domain, args->v0.signal, in nvkm_perfmon_mthd_query_source()
554 args->v0.iter); in nvkm_perfmon_mthd_query_source()
559 sig = nvkm_perfsig_find(pm, args->v0.domain, args->v0.signal, &dom); in nvkm_perfmon_mthd_query_source()
[all …]
|
| /linux/arch/powerpc/crypto/ |
| H A D | crc32-vpmsum_core.S | 157 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 D | uchan.c | 50 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 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
|