/openbmc/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 …]
|
/openbmc/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 | aes-ce-ccm-core.S | 30 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 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 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 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 …]
|
/openbmc/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 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 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 …]
|
/openbmc/linux/drivers/gpu/drm/nouveau/nvkm/engine/disp/ |
H A D | uoutp.c | 36 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 D | uconn.c | 38 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 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 …]
|
/openbmc/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 …]
|
/openbmc/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 …]
|
/openbmc/qemu/tests/tcg/xtensa/ |
H A D | fpu.h | 49 .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 D | modules.txt | 1 # 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 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 …]
|
/openbmc/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 …]
|
/openbmc/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 …]
|
/openbmc/linux/drivers/gpu/drm/amd/amdkfd/ |
H A D | cwsr_trap_handler_gfx10.asm | 380 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 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 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 D | lowlevel_init_luton.S | 24 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 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 …]
|
/openbmc/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
|