Home
last modified time | relevance | path

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

12345678910>>...16

/openbmc/linux/drivers/gpu/drm/nouveau/nvkm/core/
H A Dioctl.c83 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 …]
/openbmc/linux/arch/arm64/crypto/
H 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 …]
H 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 …]
H A Dsm4-ce-core.S52 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
428 eor v0.16b, v0.16b, v8.16b
500 eor v0.16b, v0.16b, v8.16b
533 eor v0.16b, v0.16b, v8.16b
604 eor v0.16b, v0.16b, v8.16b
636 eor v0.16b, v0.16b, v8.16b
[all …]
H A Daes-modes.S196 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 …]
/openbmc/linux/drivers/gpu/drm/nouveau/nvkm/engine/device/
H 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 …]
H 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 snprintf(args->v0.chip, sizeof(args->v0.chip), "%s", device->chip->name); in nvkm_udevice_info()
165 snprintf(args->v0.name, sizeof(args->v0.name), "%s", device->name); in nvkm_udevice_info()
387 struct nv_device_v0 v0; in nvkm_udevice_new() member
398 args->v0.version, args->v0.device); in nvkm_udevice_new()
403 if (args->v0.priv) in nvkm_udevice_new()
[all …]
/openbmc/linux/drivers/gpu/drm/nouveau/
H A Dnouveau_usif.c55 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 …]
/openbmc/linux/drivers/gpu/drm/nouveau/nvkm/engine/disp/
H A Duoutp.c36 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_dp_mst_vcpi()
41 ior->func->dp->vcpi(ior, args->v0.head, args->v0.start_slot, args->v0.num_slots, in nvkm_uoutp_mthd_dp_mst_vcpi()
42 args->v0.pbn, args->v0.aligned_pbn); in nvkm_uoutp_mthd_dp_mst_vcpi()
65 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_dp_aux_pwr()
79 if (argc < sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_hda_eld()
92 ior->func->hda->eld(ior, args->v0.head, args->v0.data, argc); in nvkm_uoutp_mthd_hda_eld()
109 if (argc < sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_infoframe()
116 ior->func->hdmi->infoframe_avi(ior, args->v0.head, &args->v0.data, size); in nvkm_uoutp_mthd_infoframe()
215 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_acquire()
261 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uoutp_mthd_load_detect()
[all …]
H A Duconn.c38 args.v0.version = 0; in nvkm_uconn_uevent_aux()
39 args.v0.types = 0; in nvkm_uconn_uevent_aux()
55 args.v0.version = 0; in nvkm_uconn_uevent_gpio()
56 args.v0.types = 0; in nvkm_uconn_uevent_gpio()
92 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uconn_uevent()
130 if (argc != sizeof(args->v0) || args->v0.version != 0) in nvkm_uconn_mthd_hpd_status()
134 args->v0.present = 0; in nvkm_uconn_mthd_hpd_status()
136 if (args->v0.support) { in nvkm_uconn_mthd_hpd_status()
140 args->v0.support = false; in nvkm_uconn_mthd_hpd_status()
144 args->v0.present = ret; in nvkm_uconn_mthd_hpd_status()
[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 …]
/openbmc/linux/drivers/gpu/drm/nouveau/nvkm/subdev/mmu/
H 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 …]
H A Duvmm.c56 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 …]
/openbmc/linux/arch/mips/include/asm/mach-cavium-octeon/
H 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 …]
/openbmc/qemu/tests/tcg/xtensa/
H A Dfpu.h49 .macro test_op1_rm op, fr0, fr1, v0, r, sr
52 movfp \fr0, \v0
57 .macro test_op2_rm op, fr0, fr1, fr2, v0, v1, r, sr
60 movfp \fr0, \v0
69 movfp \fr0, \v0
76 .macro test_op1_ex op, fr0, fr1, v0, rm, r, sr
79 test_op1_rm \op, \fr0, \fr1, \v0, \r, \sr
82 test_op1_rm \op, \fr0, \fr1, \v0, \r, \sr
104 test_op1_ex \op, \fr0, \fr1, \v0, 0, \r0, \sr0
105 test_op1_ex \op, \fr0, \fr1, \v0, 1, \r1, \sr1
[all …]
/openbmc/openbmc/meta-openembedded/meta-oe/recipes-extended/minio/minio/
H A Dmodules.txt1 # github.com/charmbracelet/bubbletea v0.19.3
11 # github.com/goccy/go-json v0.8.1
23 # github.com/mattn/go-ieproxy v0.0.1
25 # github.com/mattn/go-isatty v0.0.14
41 # github.com/minio/selfupdate v0.4.0
47 # github.com/pkg/xattr v0.4.4
69 # golang.org/x/text v0.3.7
123 # github.com/kr/text v0.2.0
153 # github.com/muesli/reflow v0.3.0
161 # github.com/pkg/errors v0.9.1
[all …]
/openbmc/linux/tools/testing/selftests/powerpc/math/
H 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 …]
/openbmc/linux/arch/arm64/lib/
H A Dxor-neon.c30 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 …]
/openbmc/linux/lib/
H A Dsiphash.c37 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 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 …]
/openbmc/linux/drivers/gpu/drm/amd/amdkfd/
H A Dcwsr_trap_handler_gfx10.asm380 v_mov_b32 v0, 0x0
632 v_mbcnt_hi_u32_b32 v0, -1, v0
633 v_mul_u32_u24 v0, 4, v0
653 v_add_nc_u32 v0, v0, 128 //mem offset increased by 128 bytes
671 v_add_nc_u32 v0, v0, 256 //mem offset increased by 256 bytes
710 v_movrels_b32 v0, v0 //v0 = v[0+m0]
736 v_movrels_b32 v0, v0 //v0 = v[0+m0]
763 v_movrels_b32 v0, v0 //v0 = v[0+m0]
887 v_movreld_b32 v0, v0 //v[0+m0] = v0
921 v_movreld_b32 v0, v0 //v[0+m0] = v0
[all …]
/openbmc/linux/drivers/gpu/drm/nouveau/nvkm/engine/pm/
H 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 …]
/openbmc/u-boot/arch/mips/mach-mscc/
H A Dlowlevel_init_luton.S24 lw v0, MACRO_CTRL_PLL5G_STATUS_PLL5G_STATUS0
25 andi v1, v0, MACRO_CTRL_PLL5G_STATUS_PLL5G_STATUS0_LOCK_STATUS
43 2: lw v0, MACRO_CTRL_PLL5G_STATUS_PLL5G_STATUS0
44 andi v1, v0, MACRO_CTRL_PLL5G_STATUS_PLL5G_STATUS0_LOCK_STATUS
50 1: lw v0, MACRO_CTRL_PLL5G_CFG_PLL5G_CFG0
54 and v0, v0, v1
57 ori v0, v0, MACRO_CTRL_PLL5G_CFG_PLL5G_CFG0_CPU_CLK_DIV_ENC(6)
59 sw v0, MACRO_CTRL_PLL5G_CFG_PLL5G_CFG0
/openbmc/linux/arch/powerpc/crypto/
H A Dcrc32-vpmsum_core.S157 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 …]
/openbmc/linux/arch/mips/lib/
H A Dstrncpy_user.S38 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

12345678910>>...16