Home
last modified time | relevance | path

Searched +full:r +full:- +full:tile (Results 1 – 25 of 36) sorted by relevance

12

/linux/arch/arm/mach-versatile/
H A DKconfig1 # SPDX-License-Identifier: GPL-2.0
48 Include support for the ARM(R) Integrator/AP and
52 bool "Include support for Integrator/IM-PD1"
60 The IM-PD1 is an add-on logic module for the Integrator which
61 allows ARM(R) Ltd PrimeCells to be developed and evaluated.
62 The IM-PD1 can be found on the Integrator/PP2 platform.
77 bool "Integrator/CM922T-XA10 core module"
83 bool "Integrator/CM926EJ-S core module"
107 bool "Integrator/CM1026EJ-S core module"
113 bool "Integrator/CM1136JF-S core module"
[all …]
/linux/drivers/gpu/drm/msm/disp/dpu1/
H A Dmsm_media_info.h5 #define MSM_MEDIA_ALIGN(__sz, __align) (((__align) & ((__align) - 1)) ?\
6 ((((__sz) + (__align) - 1) / (__align)) * (__align)) :\
7 (((__sz) + (__align) - 1) & (~((__align) - 1))))
11 #define MSM_MEDIA_ROUNDUP(__sz, __r) (((__sz) + ((__r) - 1)) / (__r))
24 * <-------- Y/UV_Stride -------->
25 * <------- Width ------->
44 * . . . . . . . . . . . . . . . . --> Buffer size alignment
50 * Extradata: Arbitrary (software-imposed) padding
62 * <-------- Y/UV_Stride -------->
63 * <------- Width ------->
[all …]
/linux/include/uapi/drm/
H A Ddrm_fourcc.h39 * further describe the buffer's format - for example tiling or compression.
42 * ---------
[all...]
/linux/drivers/gpu/drm/radeon/
H A Dcik.c144 * cik_get_allowed_info_register - fetch the register for the info ioctl
150 * Returns 0 for success or -EINVAL for an invalid register
172 return -EINVAL; in cik_get_allowed_info_register()
182 u32 r; in cik_didt_rreg() local
184 spin_lock_irqsave(&rdev->didt_idx_lock, flags); in cik_didt_rreg()
186 r = RREG32(CIK_DIDT_IND_DATA); in cik_didt_rreg()
187 spin_unlock_irqrestore(&rdev->didt_idx_lock, flags); in cik_didt_rreg()
188 return r; in cik_didt_rreg()
195 spin_lock_irqsave(&rdev->didt_idx_lock, flags); in cik_didt_wreg()
198 spin_unlock_irqrestore(&rdev->didt_idx_lock, flags); in cik_didt_wreg()
[all …]
H A Devergreen_cs.c124 track->cb_color_fmask_bo[i] = NULL; in evergreen_cs_track_init()
125 track->cb_color_cmask_bo[i] = NULL; in evergreen_cs_track_init()
126 track->cb_color_cmask_slice[i] = 0; in evergreen_cs_track_init()
127 track->cb_color_fmask_slice[i] = 0; in evergreen_cs_track_init()
131 track->cb_color_bo[i] = NULL; in evergreen_cs_track_init()
132 track->cb_color_bo_offset[i] = 0xFFFFFFFF; in evergreen_cs_track_init()
133 track->cb_color_info[i] = 0; in evergreen_cs_track_init()
134 track->cb_color_view[i] = 0xFFFFFFFF; in evergreen_cs_track_init()
135 track->cb_color_pitch[i] = 0; in evergreen_cs_track_init()
136 track->cb_color_slice[i] = 0xfffffff; in evergreen_cs_track_init()
[all …]
H A Dr600_cs.c110 /* 16-bit */
120 /* 24-bit */
123 /* 32-bit */
143 /* 48-bit */
147 /* 64-bit */
157 /* 128-bit */
170 [V_038004_FMT_BC6] = { 4, 4, 16, 0, CHIP_CEDAR}, /* Evergreen-only */
171 [V_038004_FMT_BC7] = { 4, 4, 16, 0, CHIP_CEDAR}, /* Evergreen-only */
256 u32 macro_tile_width = values->nbanks; in r600_get_array_mode_alignment()
257 u32 macro_tile_height = values->npipes; in r600_get_array_mode_alignment()
[all …]
H A Dradeon_kms.c51 * radeon_driver_unload_kms - Main unload function for KMS.
63 struct radeon_device *rdev = dev->dev_private; in radeon_driver_unload_kms()
68 if (rdev->rmmio == NULL) in radeon_driver_unload_kms()
72 pm_runtime_get_sync(dev->dev); in radeon_driver_unload_kms()
73 pm_runtime_forbid(dev->dev); in radeon_driver_unload_kms()
81 if (rdev->agp) in radeon_driver_unload_kms()
82 arch_phys_wc_del(rdev->agp->agp_mtrr); in radeon_driver_unload_kms()
83 kfree(rdev->agp); in radeon_driver_unload_kms()
84 rdev->agp = NULL; in radeon_driver_unload_kms()
88 dev->dev_private = NULL; in radeon_driver_unload_kms()
[all …]
H A Datombios_crtc.c2 * Copyright 2007-8 Advanced Micro Devices, Inc.
36 #include "atom-bits.h"
42 struct drm_device *dev = crtc->dev; in atombios_overscan_setup()
43 struct radeon_device *rdev = dev->dev_private; in atombios_overscan_setup()
51 args.ucCRTC = radeon_crtc->crtc_id; in atombios_overscan_setup()
53 switch (radeon_crtc->rmx_type) { in atombios_overscan_setup()
55 args.usOverscanTop = cpu_to_le16((adjusted_mode->crtc_vdisplay - mode->crtc_vdisplay) / 2); in atombios_overscan_setup()
56 args.usOverscanBottom = cpu_to_le16((adjusted_mode->crtc_vdisplay - mode->crtc_vdisplay) / 2); in atombios_overscan_setup()
57 args.usOverscanLeft = cpu_to_le16((adjusted_mode->crtc_hdisplay - mode->crtc_hdisplay) / 2); in atombios_overscan_setup()
58 args.usOverscanRight = cpu_to_le16((adjusted_mode->crtc_hdisplay - mode->crtc_hdisplay) / 2); in atombios_overscan_setup()
[all …]
/linux/drivers/gpu/drm/amd/display/amdgpu_dm/
H A Damdgpu_dm_plane.c1 // SPDX-License-Identifier: MIT
97 return amdgpu_lookup_format_info(cmd->pixel_format, cmd->modifier[0]); in amdgpu_dm_plane_get_format_info()
110 if (plane_state->pixel_blend_mode == DRM_MODE_BLEND_PREMULTI || in amdgpu_dm_plane_fill_blending_from_plane_state()
111 plane_state->pixel_blend_mode == DRM_MODE_BLEND_COVERAGE) { in amdgpu_dm_plane_fill_blending_from_plane_state()
122 uint32_t format = plane_state->fb->format->format; in amdgpu_dm_plane_fill_blending_from_plane_state()
132 if (*per_pixel_alpha && plane_state->pixel_blend_mode == DRM_MODE_BLEND_COVERAGE) in amdgpu_dm_plane_fill_blending_from_plane_state()
136 if (plane_state->alpha < 0xffff) { in amdgpu_dm_plane_fill_blending_from_plane_state()
138 *global_alpha_value = plane_state->alpha >> 8; in amdgpu_dm_plane_fill_blending_from_plane_state()
147 if (*cap - *size < 1) { in amdgpu_dm_plane_add_modifier()
177 return AMD_FMT_MOD_GET(TILE, modifier); in amdgpu_dm_plane_modifier_gfx9_swizzle_mode()
[all …]
/linux/drivers/gpu/drm/
H A Ddrm_connector.c52 * Hence they are reference-counted using drm_connector_get() and
68 * For connectors which are not fixed (like built-in panels) the driver needs to
77 * Note drm_connector_[un]register() first take connector->lock and then
95 { DRM_MODE_CONNECTOR_DVII, "DVI-I" },
96 { DRM_MODE_CONNECTOR_DVID, "DVI-D" },
97 { DRM_MODE_CONNECTOR_DVIA, "DVI-A" },
104 { DRM_MODE_CONNECTOR_HDMIA, "HDMI-A" },
105 { DRM_MODE_CONNECTOR_HDMIB, "HDMI-B" },
133 * drm_get_connector_type_name - return a string for connector type
148 * drm_connector_get_cmdline_mode - reads the user's cmdline mode
[all …]
H A Ddrm_edid.c3 * Copyright (c) 2007-2008 Intel Corporation
24 * FITNESS FOR A PARTICULAR PURPOSE AND NON-INFRINGEMENT. IN NO EVENT SHALL
83 /* Force reduced-blanking timings for detailed modes */
131 EDID_QUIRK('A', 'C', 'R', 44358, EDID_QUIRK_PREFER_LARGE_60),
141 /* BOE model on HP Pavilion 15-n233sl reports 8 bpc, but is a 6 bpc panel */
147 /* SDC panel of Lenovo B50-80 reports 8 bpc, but is a 6 bpc panel */
157 /* Envision Peripherals, Inc. EN-7100e */
175 /* LG Philips LCD LP154W01-A5 */
181 /* Samsung SyncMaster 22[5-6]BW */
185 /* Sony PVM-2541A does up to 12 bpc, but only reports max 8 bpc */
[all …]
/linux/Documentation/accel/amdxdna/
H A Damdnpu.rst1 .. SPDX-License-Identifier: GPL-2.0-only
15 AMD NPU (Neural Processing Unit) is a multi-user AI inference accelerator
27 --------------
31 row of memory tile. Each compute tile contains a VLIW processor with its own
32 dedicated program and data memory. The memory tile acts as L2 memory. The 2D
37 memory tile.
44 ----------------
52 ---------------
58 NPU Firmware uses a dedicated instance of an isolated non-privileged context
66 ---------
[all …]
/linux/Documentation/userspace-api/
H A Ddma-buf-alloc-exchange.rst1 .. SPDX-License-Identifier: GPL-2.0
2 .. Copyright 2021-2023 Collabora Ltd.
9 support for sharing pixel-buffer allocations between processes, devices, and
12 approach this sharing for two-dimensional image data.
25 Conceptually a two-dimensional array of pixels. The pixels may be stored
30 A span along a single y-axis value, e.g. from co-ordinates (0,100) to
37 A span along a single x-axis value, e.g. from co-ordinates (100,0) to
46 A two-dimensional array of some or all of an image's color and alpha
51 more color channels values, e.g. R, G and B, or Y, Cb and Cr. May also
65 channels R, G, and B. Alpha channel is sometimes counted as a color
[all …]
/linux/include/drm/
H A Ddrm_connector.h58 DRM_FORCE_ON_DIGITAL, /* for DVI-I use digital connector */
62 * enum drm_connector_status - status for a &drm_connector
77 * nothing there. It is driver-dependent whether a connector with this
84 * flicker (like load-detection when the connector is in use), or when a
85 * hardware resource isn't available (like when load-detection needs a
95 * enum drm_connector_registration_state - userspace registration status for
128 * - An unregistered connector may only have its DPMS changed from
129 * On->Off. Once DPMS is changed to Off, it may not be switched back
131 * - Modesets are not allowed on unregistered connectors, unless they
135 * - Removing a CRTC from an unregistered connector is OK, but new
[all …]
/linux/drivers/gpu/drm/amd/amdgpu/
H A Damdgpu_display.c2 * Copyright 2007-8 Advanced Micro Devices, Inc.
52 * amdgpu_display_hotplug_work_func - work handler for display hotplug event
72 struct drm_mode_config *mode_config = &dev->mode_config; in amdgpu_display_hotplug_work_func()
76 mutex_lock(&mode_config->mutex); in amdgpu_display_hotplug_work_func()
81 mutex_unlock(&mode_config->mutex); in amdgpu_display_hotplug_work_func()
98 schedule_work(&work->flip_work.work); in amdgpu_display_flip_callback()
111 if (!dma_fence_add_callback(fence, &work->cb, in amdgpu_display_flip_handle_fence()
125 struct amdgpu_device *adev = work->adev; in amdgpu_display_flip_work_func()
126 struct amdgpu_crtc *amdgpu_crtc = adev->mode_info.crtcs[work->crtc_id]; in amdgpu_display_flip_work_func()
128 struct drm_crtc *crtc = &amdgpu_crtc->base; in amdgpu_display_flip_work_func()
[all …]
/linux/drivers/gpu/drm/pl111/
H A Dpl111_versatile.c1 // SPDX-License-Identifier: GPL-2.0-only
5 * This is based on code and know-how in the previous frame buffer
6 * driver in drivers/video/fbdev/amba-clcd.c:
46 .compatible = "arm,core-module-integrator",
50 .compatible = "arm,versatile-sysreg",
54 .compatible = "arm,realview-eb-syscon",
58 .compatible = "arm,realview-pb1176-syscon",
62 .compatible = "arm,realview-pb11mp-syscon",
66 .compatible = "arm,realview-pba8-syscon",
70 .compatible = "arm,realview-pbx-syscon",
[all …]
/linux/drivers/gpu/drm/nouveau/nvkm/engine/gr/
H A Dgf100.h40 #define ROP_BCAST(r) (0x408800 + (r)) argument
41 #define ROP_UNIT(u, r) (0x410000 + (u) * 0x400 + (r)) argument
42 #define GPC_BCAST(r) (0x418000 + (r)) argument
43 #define GPC_UNIT(t, r) (0x500000 + (t) * 0x8000 + (r)) argument
44 #define PPC_UNIT(t, m, r) (0x503000 + (t) * 0x8000 + (m) * 0x200 + (r)) argument
45 #define TPC_UNIT(t, m, r) (0x504000 + (t) * 0x8000 + (m) * 0x800 + (r)) argument
124 u8 tile[TPC_MAX]; member
313 for (pack = head; pack && pack->init; pack++) \
314 for (init = pack->init; init && init->count; init++)
/linux/arch/riscv/kernel/
H A Dptrace.c1 // SPDX-License-Identifier: GPL-2.0-only
7 * Copied from arch/tile/kernel/ptrace.c
52 return user_regset_copyin(&pos, &count, &kbuf, &ubuf, regs, 0, -1); in riscv_gpr_set()
60 struct __riscv_d_ext_state *fstate = &target->thread.fstate; in riscv_fpr_get()
66 membuf_store(&to, fstate->fcsr); in riscv_fpr_get()
76 struct __riscv_d_ext_state *fstate = &target->thread.fstate; in riscv_fpr_set()
83 sizeof(fstate->fcsr)); in riscv_fpr_set()
95 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_get()
99 return -EINVAL; in riscv_vr_get()
107 riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current)); in riscv_vr_get()
[all …]
/linux/include/asm-generic/
H A Dtlb.h1 /* SPDX-License-Identifier: GPL-2.0-or-later */
2 /* include/asm-generic/tlb.h
32 * Generic MMU-gather implementation.
49 * - tlb_gather_mmu() / tlb_gather_mmu_fullmm() / tlb_finish_mmu()
56 * - tlb_start_vma() / tlb_end_vma(); marks the start / end of a VMA
61 * - tlb_remove_table()
63 * tlb_remove_table() is the basic primitive to free page-table directories
70 * - tlb_remove_page() / tlb_remove_page_size()
71 * - __tlb_remove_folio_pages() / __tlb_remove_page_size()
72 * - __tlb_remove_folio_pages_size()
[all …]
/linux/drivers/gpu/drm/sun4i/
H A Dsun4i_frontend.c1 // SPDX-License-Identifier: GPL-2.0+
4 * Maxime Ripard <maxime.ripard@free-electrons.com>
59 * The first three values of each row are coded as 13-bit signed fixed-point
61 * constant coded as a 14-bit signed fixed-point number with 4 bits for the
65 * G = 1.164 * Y - 0.391 * U - 0.813 * V + 135
66 * R = 1.164 * Y + 1.596 * V - 222
83 if (frontend->data->has_coef_access_ctrl) in sun4i_frontend_scaler_init()
84 regmap_write_bits(frontend->regs, SUN4I_FRONTEND_FRM_CTRL_REG, in sun4i_frontend_scaler_init()
89 regmap_write(frontend->regs, SUN4I_FRONTEND_CH0_HORZCOEF0_REG(i), in sun4i_frontend_scaler_init()
91 regmap_write(frontend->regs, SUN4I_FRONTEND_CH1_HORZCOEF0_REG(i), in sun4i_frontend_scaler_init()
[all …]
/linux/drivers/media/platform/mediatek/mdp3/
H A Dmtk-mdp3-regs.h1 /* SPDX-License-Identifier: GPL-2.0-only */
4 * Author: Ping-Hsun Wu <ping-hsun.wu@mediatek.com>
11 #include <media/videobuf2-core.h>
12 #include "mtk-img-ipi.h"
17 * H-subsample: 0, 1, 2
18 * V-subsample: 0, 1
19 * Color group: 0-RGB, 1-YUV, 2-raw
107 /* For bayer+mono raw-16 */
159 /* Packed 10-bit formats */
162 /* Packed 10-bit UYVY */
[all …]
/linux/drivers/pinctrl/qcom/
H A Dpinctrl-sc8180x.c1 // SPDX-License-Identifier: GPL-2.0
3 * Copyright (c) 2018-2019, The Linux Foundation. All rights reserved.
4 * Copyright (c) 2020-2021, Linaro Ltd.
11 #include "pinctrl-msm.h"
64 .tile = _tile, \
94 .tile = EAST, \
95 .mux_bit = -1, \
98 .oe_bit = -1, \
99 .in_bit = -1, \
100 .out_bit = -1, \
[all …]
/linux/arch/x86/kvm/
H A Dcpuid.c1 // SPDX-License-Identifier: GPL-2.0-only
3 * Kernel-based Virtual Machine driver for Linux
55 cpuid_count(0xD, i, &xs->eax, &xs->ebx, &xs->ecx, &ign); in kvm_init_xstate_sizes()
74 offset = (xs->ecx & 0x2) ? ALIGN(ret, 64) : ret; in xstate_required_size()
76 offset = xs->ebx; in xstate_required_size()
77 ret = max(ret, offset + xs->eax); in xstate_required_size()
85 * Magic value used by KVM when querying userspace-provided CPUID entries and
91 #define KVM_CPUID_INDEX_NOT_SIGNIFICANT -1ull
100 * KVM has a semi-arbitrary rule that querying the guest's CPUID model in cpuid_entry2_find()
104 * path, e.g. the core VM-Enter/VM-Exit run loop. Nothing will break in cpuid_entry2_find()
[all …]
/linux/include/uapi/linux/
H A Dkfd_ioctl.h30 * - 1.1 - initial version
31 * - 1.3 - Add SMI events support
32 * - 1.4 - Indicate new SRAM EDC bit in device properties
33 * - 1.5 - Add SVM API
34 * - 1.6 - Quer
[all...]
/linux/mm/
H A Dmm_init.c1 // SPDX-License-Identifier: GPL-2.0-only
3 * mm_init.c - Memory initialisation verification and debugging
18 #include <linux/page-isolation.h>
78 zonelist = &pgdat->node_zonelists[listid]; in mminit_verify_zonelist()
79 zone = &pgdat->node_zones[zoneid]; in mminit_verify_zonelist()
86 zone->name); in mminit_verify_zonelist()
90 pr_cont("%d:%s ", zone_to_nid(zone), zone->name); in mminit_verify_zonelist()
102 width = shift - NR_NON_PAGEFLAG_BITS; in mminit_verify_pageflags_layout()
128 "Node/Zone ID: %lu -> %lu\n", in mminit_verify_pageflags_layout()
132 "location: %d -> %d layout %d -> %d unused %d -> %d page-flags\n", in mminit_verify_pageflags_layout()
[all …]

12