Home
last modified time | relevance | path

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

1234567891011

/linux/drivers/gpu/drm/nouveau/nvkm/core/
A Dioctl.c62 args->v0.version, args->v0.count); in nvkm_ioctl_sclass()
97 args->v0.version, args->v0.handle, args->v0.oclass, in nvkm_ioctl_new()
98 args->v0.route, args->v0.token, args->v0.object); in nvkm_ioctl_new()
176 args->v0.version, args->v0.method); in nvkm_ioctl_mthd()
201 args->v0.version, args->v0.size, args->v0.addr); in nvkm_ioctl_rd()
237 args->v0.version, args->v0.size, args->v0.addr, in nvkm_ioctl_wr()
309 args->v0.version, args->v0.event); in nvkm_ioctl_ntfy_new()
335 args->v0.version, args->v0.index); in nvkm_ioctl_ntfy_del()
354 args->v0.version, args->v0.index); in nvkm_ioctl_ntfy_get()
373 args->v0.version, args->v0.index); in nvkm_ioctl_ntfy_put()
[all …]
A Dclient.c39 struct nvif_client_v0 v0; in nvkm_uclient_new() member
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()
155 req->v0.reply, req->v0.route, req->v0.token); in nvkm_client_notify_new()
158 notify->rep.v0.version = req->v0.version; in nvkm_client_notify_new()
159 notify->rep.v0.route = req->v0.route; in nvkm_client_notify_new()
160 notify->rep.v0.token = req->v0.token; in nvkm_client_notify_new()
161 reply = req->v0.reply; in nvkm_client_notify_new()
202 args->v0.version, args->v0.count); in nvkm_client_mthd_devlist()
203 if (size == sizeof(args->v0.device[0]) * args->v0.count) { in nvkm_client_mthd_devlist()
[all …]
/linux/drivers/gpu/drm/nouveau/nvkm/engine/disp/
A Drootnv50.c56 args->v0.version, args->v0.method, args->v0.head); in nv50_disp_root_mthd_()
58 hidx = args->v0.head; in nv50_disp_root_mthd_()
180 args->v0.version, args->v0.state, in nv50_disp_root_mthd_()
181 args->v0.max_ac_packet, args->v0.rekey, in nv50_disp_root_mthd_()
182 args->v0.scdc); in nv50_disp_root_mthd_()
183 if (args->v0.max_ac_packet > 0x1f || args->v0.rekey > 0x7f) in nv50_disp_root_mthd_()
222 args->v0.version, args->v0.script); in nv50_disp_root_mthd_()
238 args->v0.version, args->v0.state); in nv50_disp_root_mthd_()
254 args->v0.version, args->v0.start_slot, in nv50_disp_root_mthd_()
255 args->v0.num_slots, args->v0.pbn, in nv50_disp_root_mthd_()
[all …]
A Dhead.c47 struct nv04_disp_scanoutpos_v0 v0; in nvkm_head_mthd_scanoutpos() member
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()
71 args->v0.time[0] = ktime_to_ns(ktime_get()); in nvkm_head_mthd_scanoutpos()
[all …]
/linux/arch/arm64/crypto/
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 …]
A Daes-ce-ccm-core.S30 eor v0.16b, v0.16b, v1.16b
43 aesmc v0.16b, v0.16b
46 aesmc v0.16b, v0.16b
50 aesmc v0.16b, v0.16b
79 91: eor v0.16b, v0.16b, v1.16b
102 aesmc v0.16b, v0.16b
107 aesmc v0.16b, v0.16b
113 aesmc v0.16b, v0.16b
148 aesmc v0.16b, v0.16b
153 aesmc v0.16b, v0.16b
[all …]
A Daes-modes.S203 eor v0.16b, v0.16b, cbciv.16b
272 tbl v0.16b, {v0.16b}, v3.16b
397 eor v0.16b, v5.16b, v0.16b
519 eor v0.16b, v0.16b, v4.16b
527 eor v0.16b, v0.16b, v4.16b
543 eor v0.16b, v0.16b, v4.16b
545 eor v0.16b, v0.16b, v4.16b
612 eor v0.16b, v0.16b, v4.16b
620 eor v0.16b, v0.16b, v4.16b
636 eor v0.16b, v0.16b, v4.16b
[all …]
/linux/drivers/gpu/drm/nouveau/nvkm/engine/device/
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 …]
A Duser.c80 struct nv_device_info_v0 v0; in nvkm_udevice_info() member
151 args->v0.family = 0; in nvkm_udevice_info()
158 args->v0.ram_size = args->v0.ram_user = fb->ram->size; in nvkm_udevice_info()
160 args->v0.ram_size = args->v0.ram_user = 0; in nvkm_udevice_info()
162 args->v0.ram_user = args->v0.ram_user - imem->reserved; in nvkm_udevice_info()
164 strncpy(args->v0.chip, device->chip->name, sizeof(args->v0.chip)); in nvkm_udevice_info()
165 strncpy(args->v0.name, device->name, sizeof(args->v0.name)); in nvkm_udevice_info()
384 struct nv_device_v0 v0; in nvkm_udevice_new() member
395 args->v0.version, args->v0.device); in nvkm_udevice_new()
400 if (args->v0.priv) in nvkm_udevice_new()
[all …]
/linux/drivers/gpu/drm/nouveau/
A Dnouveau_usif.c86 if (length == sizeof(rep->v0) && rep->v0.version == 0) { in usif_notify()
101 switch (rep->v0.version) { in usif_notify()
280 switch (args->v0.oclass) { in usif_object_new()
287 struct nv_device_v0 v0; in usif_object_new() member
293 args->v0.priv = false; in usif_object_new()
329 struct nvif_ioctl_v0 v0; in usif_ioctl() member
343 owner = argv->v0.owner; in usif_ioctl()
356 if (argv->v0.route) { in usif_ioctl()
367 switch (argv->v0.type) { in usif_ioctl()
397 argv->v0.token = 0; in usif_ioctl()
[all …]
/linux/drivers/gpu/drm/nouveau/nvkm/subdev/mmu/
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 …]
A Duvmm.c56 addr = args->v0.addr; in nvkm_uvmm_mthd_pfnclr()
57 size = args->v0.size; in nvkm_uvmm_mthd_pfnclr()
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()
112 addr = args->v0.addr; in nvkm_uvmm_mthd_unmap()
155 addr = args->v0.addr; in nvkm_uvmm_mthd_map()
156 size = args->v0.size; in nvkm_uvmm_mthd_map()
398 args->v0.page_nr = 0; in nvkm_uvmm_new()
[all …]
/linux/lib/
A Dsiphash.c23 v0 += v1; v1 = rol64(v1, 13); v1 ^= v0; v0 = rol64(v0, 32); \
25 v0 += v3; v3 = rol64(v3, 21); v3 ^= v0; \
44 v0 ^= b; \
64 v0 ^= m; in __siphash_aligned()
97 v0 ^= m; in __siphash_unaligned()
264 v0 ^= m; in __hsiphash_aligned()
297 v0 ^= m; in __hsiphash_unaligned()
394 v0 += v1; v1 = rol32(v1, 5); v1 ^= v0; v0 = rol32(v0, 16); \
396 v0 += v3; v3 = rol32(v3, 7); v3 ^= v0; \
432 v0 ^= m; in __hsiphash_aligned()
[all …]
A Drandom32.c366 unsigned long v0 = s->v0, v1 = s->v1, v2 = s->v2, v3 = s->v3; in siprand_u32() local
372 v0 ^= n; in siprand_u32()
373 s->v0 = v0; s->v1 = v1; s->v2 = v2; s->v3 = v3; in siprand_u32()
441 unsigned long v0 = state->v0, v1 = state->v1; in prandom_seed() local
451 WRITE_ONCE(state->v0, v0); in prandom_seed()
469 v0 = jiffies; in prandom_init_early()
481 v0 ^= i; in prandom_init_early()
484 state->v0 = v0; state->v1 = v1; in prandom_init_early()
510 unsigned long v0 = get_random_long(), v2 = v0 ^ PRND_K0; in prandom_reseed() local
527 v0 ^= m; in prandom_reseed()
[all …]
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/mips/include/asm/mach-cavium-octeon/
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/drivers/gpu/drm/nouveau/nvkm/engine/fifo/
A Dgpfifotu102.c57 struct volta_channel_gpfifo_a_v0 v0; in tu102_fifo_gpfifo_new() member
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()
75 args->v0.priv, in tu102_fifo_gpfifo_new()
[all …]
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()
A Dgpfifog84.c39 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/tools/testing/selftests/powerpc/math/
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/arch/arm64/lib/
A Dxor-neon.c19 register uint64x2_t v0, v1, v2, v3; in xor_arm64_neon_2() local
30 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_2()
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()
94 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_4()
100 v0 = veorq_u64(v0, vld1q_u64(dp4 + 0)); in xor_arm64_neon_4()
106 vst1q_u64(dp1 + 0, v0); in xor_arm64_neon_4()
139 v0 = veorq_u64(v0, vld1q_u64(dp3 + 0)); in xor_arm64_neon_5()
145 v0 = veorq_u64(v0, vld1q_u64(dp4 + 0)); in xor_arm64_neon_5()
151 v0 = veorq_u64(v0, vld1q_u64(dp5 + 0)); in xor_arm64_neon_5()
[all …]
/linux/drivers/gpu/drm/nouveau/nvkm/engine/pm/
A Dbase.c384 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 strncpy(args->v0.name, dom->name, sizeof(args->v0.name) - 1); 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()
554 args->v0.version, args->v0.domain, args->v0.signal, in nvkm_perfmon_mthd_query_source()
555 args->v0.iter); in nvkm_perfmon_mthd_query_source()
560 sig = nvkm_perfsig_find(pm, args->v0.domain, args->v0.signal, &dom); in nvkm_perfmon_mthd_query_source()
575 strncpy(args->v0.name, src->name, sizeof(args->v0.name) - 1); in nvkm_perfmon_mthd_query_source()
[all …]
/linux/arch/powerpc/crypto/
A Dcrc32-vpmsum_core.S160 vxor v0,v0,v0
259 vxor v0,v0,v8
316 vxor v0,v0,v8
350 vxor v0,v0,v8
452 vxor v0,v0,v16
459 vxor v0,v0,v16
466 vxor v0,v0,v16
473 vxor v0,v0,v16
502 vxor v0,v0,v2
505 vxor v0,v0,v4
[all …]
/linux/drivers/gpu/drm/amd/amdkfd/
A Dcwsr_trap_handler_gfx10.asm530 v_mbcnt_hi_u32_b32 v0, -1, v0
531 v_mul_u32_u24 v0, 4, v0
545 ds_read_b32 v1, v0
551 v_add_nc_u32 v0, v0, 128 //mem offset increased by 128 bytes
569 v_add_nc_u32 v0, v0, 256 //mem offset increased by 256 bytes
608 v_movrels_b32 v0, v0 //v0 = v[0+m0]
634 v_movrels_b32 v0, v0 //v0 = v[0+m0]
660 v_movrels_b32 v0, v0 //v0 = v[0+m0]
775 v_movreld_b32 v0, v0 //v[0+m0] = v0
806 v_movreld_b32 v0, v0 //v[0+m0] = v0
[all …]
/linux/include/linux/
A Dprandom.h30 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument
31 v0 += v1, v1 = rol64(v1, 13), v2 += v3, v3 = rol64(v3, 16), \
32 v1 ^= v0, v0 = rol64(v0, 32), v3 ^= v2, \
33 v0 += v3, v3 = rol64(v3, 21), v2 += v1, v1 = rol64(v1, 17), \
34 v3 ^= v0, v1 ^= v2, v2 = rol64(v2, 32) \
46 #define PRND_SIPROUND(v0, v1, v2, v3) ( \ argument
47 v0 += v1, v1 = rol32(v1, 5), v2 += v3, v3 = rol32(v3, 8), \
48 v1 ^= v0, v0 = rol32(v0, 16), v3 ^= v2, \
49 v0 += v3, v3 = rol32(v3, 7), v2 += v1, v1 = rol32(v1, 13), \
50 v3 ^= v0, v1 ^= v2, v2 = rol32(v2, 16) \

Completed in 67 milliseconds

1234567891011