Home
last modified time | relevance | path

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

12345678910>>...12

/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()
40 if (!ior->func->dp || !ior->func->dp->vcpi || !nvkm_head_find(outp->disp, args->v0.head)) 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()
58 return outp->func->dp.mst_id_put(outp, args->v0.id); 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()
71 return outp->func->dp.mst_id_get(outp, &args->v0.id); in nvkm_uoutp_mthd_dp_mst_id_get()
81 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_dp_sst()
84 if (!ior->func->dp || !nvkm_head_find(disp, args->v0.head)) in nvkm_uoutp_mthd_dp_sst()
[all …]
H A Duconn.c38 args.v0.version = 0; in nvkm_uconn_uevent_gsp()
39 args.v0.types = 0; in nvkm_uconn_uevent_gsp()
41 args.v0.types |= NVIF_CONN_EVENT_V0_PLUG; in nvkm_uconn_uevent_gsp()
43 args.v0.types |= NVIF_CONN_EVENT_V0_UNPLUG; in nvkm_uconn_uevent_gsp()
45 args.v0.types |= NVIF_CONN_EVENT_V0_IRQ; in nvkm_uconn_uevent_gsp()
47 return object->client->event(token, &args, sizeof(args.v0)); 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()
58 args.v0.types |= NVIF_CONN_EVENT_V0_PLUG; in nvkm_uconn_uevent_aux()
60 args.v0.types |= NVIF_CONN_EVENT_V0_UNPLUG; in nvkm_uconn_uevent_aux()
[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]
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 Dsm4-ce-core.S51 ld1 {v0.16b}, [x0];
52 rev32 v0.16b, v0.16b;
59 eor v0.16b, v0.16b, v1.16b;
61 sm4ekey v0.4s, v0.4s, v24.4s;
62 sm4ekey v1.4s, v0.4s, v25.4s;
73 st1 {v0.16b-v3.16b}, [x1], #64;
83 tbl v23.16b, {v0.16b}, v24.16b
100 ld1 {v0.16b}, [x2];
101 SM4_CRYPT_BLK(v0);
102 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
62 ld1 {v0.16b-v3.16b}, [x1], #64 /* get 4 pt blocks */
66 st1 {v0.16b-v3.16b}, [x0], #64
73 ld1 {v0.16b}, [x1], #16 /* get next pt block */
74 encrypt_block v0, w3, x2, x5, w6
75 st1 {v0.16b}, [x0], #16
92 ld1 {v0.16b-v3.16b}, [x1], #64 /* get 4 ct blocks */
[all …]
H A Dsm4-ce-gcm-core.S237 #define RR1 v0
275 rev32 v0.16b, RZERO.16b
276 SM4_CRYPT_BLK_BE(v0)
279 rbit RH1.16b, v0.16b
322 ld1 {v0.16b-v3.16b}, [x2], #64
324 rbit v0.16b, v0.16b
335 eor RHASH.16b, RHASH.16b, v0.16b
357 ld1 {v0.16b}, [x2], #16
358 rbit v0.16b, v0.16b
359 eor RHASH.16b, RHASH.16b, v0.16b
[all …]
/linux/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 …]
/linux/rust/syn/gen/
H A Dclone.rs149 crate::CapturedParam::Lifetime(v0) => { in clone()
150 crate::CapturedParam::Lifetime(v0.clone()) in clone()
152 crate::CapturedParam::Ident(v0) => crate::CapturedParam::Ident(v0.clone()), in clone()
188 crate::Data::Struct(v0) => crate::Data::Struct(v0.clone()), in clone()
189 crate::Data::Enum(v0) => crate::Data::Enum(v0.clone()), in clone()
190 crate::Data::Union(v0) => crate::Data::Union(v0.clone()), in clone()
245 crate::Expr::Array(v0) => crate::Expr::Array(v0.clone()), in clone()
247 crate::Expr::Assign(v0) => crate::Expr::Assign(v0.clone()), in clone()
249 crate::Expr::Async(v0) => crate::Expr::Async(v0.clone()), in clone()
251 crate::Expr::Await(v0) => crate::Expr::Await(v0.clone()), in clone()
[all …]
H A Dhash.rs243 crate::CapturedParam::Lifetime(v0) => { in hash()
245 v0.hash(state); in hash()
247 crate::CapturedParam::Ident(v0) => { in hash()
249 v0.hash(state); in hash()
288 crate::Data::Struct(v0) => { in hash()
290 v0.hash(state); in hash()
292 crate::Data::Enum(v0) => { in hash()
294 v0.hash(state); in hash()
296 crate::Data::Union(v0) => { in hash()
298 v0.hash(state); in hash()
[all …]
H A Ddebug.rs81 crate::AttrStyle::Inner(v0) => { in fmt()
83 formatter.field(v0); in fmt()
130 crate::BinOp::Add(v0) => { in fmt()
132 formatter.field(v0); in fmt()
135 crate::BinOp::Sub(v0) => { in fmt()
137 formatter.field(v0); in fmt()
140 crate::BinOp::Mul(v0) => { in fmt()
142 formatter.field(v0); in fmt()
145 crate::BinOp::Div(v0) => { in fmt()
147 formatter.field(v0); in fmt()
[all …]
/linux/drivers/gpu/drm/nouveau/nvkm/core/
H A Dioctl.c64 struct nvif_ioctl_sclass_v0 v0; in nvkm_ioctl_sclass() member
70 if (!(ret = nvif_unpack(ret, &data, &size, args->v0, 0, 0, true))) { in nvkm_ioctl_sclass()
72 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()
78 args->v0.oclass[i].oclass = oclass.base.oclass; in nvkm_ioctl_sclass()
79 args->v0.oclass[i].minver = oclass.base.minver; in nvkm_ioctl_sclass()
80 args->v0.oclass[i].maxver = oclass.base.maxver; in nvkm_ioctl_sclass()
85 args->v0.count = i; in nvkm_ioctl_sclass()
96 struct nvif_ioctl_new_v0 v0; in nvkm_ioctl_new() member
[all …]
/linux/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.c49 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()
77 struct nvif_vmm_pfnmap_v0 v0; in nvkm_uvmm_mthd_pfnmap() member
84 if (!(ret = nvif_unpack(ret, &argv, &argc, args->v0, 0, 0, true))) { in nvkm_uvmm_mthd_pfnmap()
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()
[all …]
/linux/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 …]
/linux/drivers/gpu/drm/amd/amdkfd/
H A Dcwsr_trap_handler_gfx10.asm429 global_store_dword_addtid v0, [s_save_ttmps_lo, s_save_ttmps_hi] V_COHERENCE
430 v_mov_b32 v0, 0x0
447 v_writelane_b32 v0, ttmp4, 0x4
448 v_writelane_b32 v0, ttmp5, 0x5
449 v_writelane_b32 v0, ttmp6, 0x6
450 v_writelane_b32 v0, ttmp7, 0x7
451 v_writelane_b32 v0, ttmp8, 0x8
452 v_writelane_b32 v0, ttmp9, 0x9
453 v_writelane_b32 v0, ttmp10, 0xA
454 v_writelane_b32 v0, ttmp11, 0xB
[all …]
H A Dcwsr_trap_handler_gfx12.asm357 global_store_dword_addtid v0, [s_save_ttmps_lo, s_save_ttmps_hi] scope:SCOPE_SYS
358 v_mov_b32 v0, 0x0
373 v_writelane_b32 v0, ttmp4, 0x4
374 v_writelane_b32 v0, ttmp5, 0x5
375 v_writelane_b32 v0, ttmp6, 0x6
376 v_writelane_b32 v0, ttmp7, 0x7
377 v_writelane_b32 v0, ttmp8, 0x8
378 v_writelane_b32 v0, ttmp9, 0x9
379 v_writelane_b32 v0, ttmp10, 0xA
380 v_writelane_b32 v0, ttmp11, 0xB
[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
31 vxor.vv v16, v0, v16
42 vle8.v v0, (a1)
45 vxor.vv v0, v0, v8
48 vxor.vv v0, v0, v16
51 vxor.vv v16, v0, v24
62 vle8.v v0, (a1)
[all …]
/linux/lib/
H A Dsiphash.c20 #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 …]
/linux/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()
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/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 …]
/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/crc/arm64/
H A Dcrc-t10dif-core.S223 CPU_LE( rev64 v0.16b, v0.16b )
231 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
243 eor v0.16b, v0.16b, v8.16b
255 fold_32_bytes \p, v0, v1
268 fold_16_bytes \p, v0, v4
291 CPU_LE( rev64 v0.16b, v0.16b )
292 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
293 eor v7.16b, v7.16b, v0.16b
313 CPU_LE( rev64 v0.16b, v0.16b )
314 CPU_LE( ext v0.16b, v0.16b, v0.16b, #8 )
[all …]
/linux/lib/crc/powerpc/
H A Dcrc-vpmsum-template.S101 vspltisw v0,-1
103 vsldoi mask_32bit,zeroes,v0,4
104 vsldoi mask_64bit,zeroes,v0,8
157 vxor v0,v0,v0
256 vxor v0,v0,v8
313 vxor v0,v0,v8
347 vxor v0,v0,v8
363 vsldoi v0,v0,zeroes,4
393 vxor v16,v0,v8
422 lvx v0,0,r3
[all …]
/linux/arch/mips/kernel/
H A Dscall32-o32.S84 subu t2, v0, __NR_O32_Linux
89 LONG_S v0, TI_SYSCALL($28) # Save v0 as syscall number
97 subu v0, v0, __NR_O32_Linux # check syscall number
98 sltiu t0, v0, __NR_O32_Linux_syscalls
101 sll t0, v0, 2
111 sltu t0, t0, v0
116 negu v0 # error
118 1: sw v0, PT_R2(sp) # result
131 bltz v0, 1f # seccomp failed? Skip syscall
134 lw v0, PT_R2(sp) # Restore syscall (maybe modified)
[all …]

12345678910>>...12