Home
last modified time | relevance | path

Searched refs:px (Results 1 - 25 of 54) sorted by relevance

123

/kernel/linux/linux-5.10/drivers/gpu/drm/i915/gt/
H A Dintel_gtt.h169 #define px_base(px) \
170 __px_choose_expr(px, struct drm_i915_gem_object *, __x, \
171 __px_choose_expr(px, struct i915_page_table *, __x->base, \
172 __px_choose_expr(px, struct i915_page_directory *, __x->pt.base, \
177 #define px_dma(px) (__px_dma(px_base(px)))
179 #define px_pt(px) \
180 __px_choose_expr(px, struct i915_page_table *, __x, \
181 __px_choose_expr(px, struct i915_page_directory *, &__x->pt, \
183 #define px_used(px) (
[all...]
/kernel/linux/linux-6.6/drivers/gpu/drm/i915/gt/
H A Dintel_gtt.h196 #define px_base(px) \
197 __px_choose_expr(px, struct drm_i915_gem_object *, __x, \
198 __px_choose_expr(px, struct i915_page_table *, __x->base, \
199 __px_choose_expr(px, struct i915_page_directory *, __x->pt.base, \
204 #define px_dma(px) (__px_dma(px_base(px)))
207 #define px_vaddr(px) (__px_vaddr(px_base(px)))
209 #define px_pt(px) \
210 __px_choose_expr(px, struc
[all...]
/kernel/linux/linux-5.10/drivers/acpi/
H A Dprocessor_perflib.c281 static void amd_fixup_frequency(struct acpi_processor_px *px, int i) in amd_fixup_frequency() argument
284 int index = px->control & 0x00000007; in amd_fixup_frequency()
302 px->core_frequency = (100 * (fid + 0x10)) >> did; in amd_fixup_frequency()
304 px->core_frequency = (100 * (fid + 8)) >> did; in amd_fixup_frequency()
308 static void amd_fixup_frequency(struct acpi_processor_px *px, int i) {}; in amd_fixup_frequency() argument
351 struct acpi_processor_px *px = &(pr->performance->states[i]); in acpi_processor_get_performance_states() local
354 state.pointer = px; in acpi_processor_get_performance_states()
367 amd_fixup_frequency(px, i); in acpi_processor_get_performance_states()
372 (u32) px->core_frequency, in acpi_processor_get_performance_states()
373 (u32) px in acpi_processor_get_performance_states()
[all...]
/kernel/linux/linux-6.6/drivers/acpi/
H A Dprocessor_perflib.c275 static void amd_fixup_frequency(struct acpi_processor_px *px, int i) in amd_fixup_frequency() argument
278 int index = px->control & 0x00000007; in amd_fixup_frequency()
296 px->core_frequency = (100 * (fid + 0x10)) >> did; in amd_fixup_frequency()
298 px->core_frequency = (100 * (fid + 8)) >> did; in amd_fixup_frequency()
302 static void amd_fixup_frequency(struct acpi_processor_px *px, int i) {}; in amd_fixup_frequency() argument
344 struct acpi_processor_px *px = &(pr->performance->states[i]); in acpi_processor_get_performance_states() local
347 state.pointer = px; in acpi_processor_get_performance_states()
361 amd_fixup_frequency(px, i); in acpi_processor_get_performance_states()
366 (u32) px->core_frequency, in acpi_processor_get_performance_states()
367 (u32) px in acpi_processor_get_performance_states()
[all...]
/kernel/linux/linux-5.10/lib/raid6/
H A Drecov_neon_inner.c39 * uint8_t px, qx, db; in __raid6_2data_recov_neon()
41 * px = *p ^ *dp; in __raid6_2data_recov_neon()
43 * *dq++ = db = pbmul[px] ^ qx; in __raid6_2data_recov_neon()
44 * *dp++ = db ^ px; in __raid6_2data_recov_neon()
50 uint8x16_t vx, vy, px, qx, db; in __raid6_2data_recov_neon() local
52 px = veorq_u8(vld1q_u8(p), vld1q_u8(dp)); in __raid6_2data_recov_neon()
60 vy = vshrq_n_u8(px, 4); in __raid6_2data_recov_neon()
61 vx = vqtbl1q_u8(pm0, vandq_u8(px, x0f)); in __raid6_2data_recov_neon()
67 vst1q_u8(dp, veorq_u8(db, px)); in __raid6_2data_recov_neon()
H A Drecov.c24 u8 px, qx, db; in raid6_2data_recov_intx1() local
55 px = *p ^ *dp; in raid6_2data_recov_intx1()
57 *dq++ = db = pbmul[px] ^ qx; /* Reconstructed B */ in raid6_2data_recov_intx1()
58 *dp++ = db ^ px; /* Reconstructed A */ in raid6_2data_recov_intx1()
/kernel/linux/linux-6.6/lib/raid6/
H A Drecov_neon_inner.c40 * uint8_t px, qx, db; in __raid6_2data_recov_neon()
42 * px = *p ^ *dp; in __raid6_2data_recov_neon()
44 * *dq++ = db = pbmul[px] ^ qx; in __raid6_2data_recov_neon()
45 * *dp++ = db ^ px; in __raid6_2data_recov_neon()
51 uint8x16_t vx, vy, px, qx, db; in __raid6_2data_recov_neon() local
53 px = veorq_u8(vld1q_u8(p), vld1q_u8(dp)); in __raid6_2data_recov_neon()
61 vy = vshrq_n_u8(px, 4); in __raid6_2data_recov_neon()
62 vx = vqtbl1q_u8(pm0, vandq_u8(px, x0f)); in __raid6_2data_recov_neon()
68 vst1q_u8(dp, veorq_u8(db, px)); in __raid6_2data_recov_neon()
H A Drecov.c23 u8 px, qx, db; in raid6_2data_recov_intx1() local
54 px = *p ^ *dp; in raid6_2data_recov_intx1()
56 *dq++ = db = pbmul[px] ^ qx; /* Reconstructed B */ in raid6_2data_recov_intx1()
57 *dp++ = db ^ px; /* Reconstructed A */ in raid6_2data_recov_intx1()
/kernel/linux/linux-5.10/drivers/gpu/drm/nouveau/nvkm/subdev/bus/
H A Dhwsq.c139 u32 heads, x, y, px = 0; in nvkm_hwsq_wait_vblank() local
149 if ((x * y) > px) { in nvkm_hwsq_wait_vblank()
150 px = (x * y); in nvkm_hwsq_wait_vblank()
156 if (px == 0) { in nvkm_hwsq_wait_vblank()
/kernel/linux/linux-6.6/drivers/gpu/drm/nouveau/nvkm/subdev/bus/
H A Dhwsq.c139 u32 heads, x, y, px = 0; in nvkm_hwsq_wait_vblank() local
149 if ((x * y) > px) { in nvkm_hwsq_wait_vblank()
150 px = (x * y); in nvkm_hwsq_wait_vblank()
156 if (px == 0) { in nvkm_hwsq_wait_vblank()
/kernel/linux/linux-5.10/drivers/gpu/drm/nouveau/nvkm/subdev/pmu/
H A Dmemx.c129 u32 heads, x, y, px = 0; in nvkm_memx_wait_vblank() local
140 if ((x * y) > px) { in nvkm_memx_wait_vblank()
141 px = (x * y); in nvkm_memx_wait_vblank()
148 if (px == 0) { in nvkm_memx_wait_vblank()
/kernel/linux/linux-6.6/drivers/gpu/drm/nouveau/nvkm/subdev/pmu/
H A Dmemx.c129 u32 heads, x, y, px = 0; in nvkm_memx_wait_vblank() local
140 if ((x * y) > px) { in nvkm_memx_wait_vblank()
141 px = (x * y); in nvkm_memx_wait_vblank()
148 if (px == 0) { in nvkm_memx_wait_vblank()
/kernel/linux/linux-5.10/drivers/iommu/
H A Ds390-iommu.c280 unsigned int rtx, sx, px; in s390_iommu_iova_to_phys() local
289 px = calc_px(iova); in s390_iommu_iova_to_phys()
297 if (pto && pt_entry_isvalid(pto[px])) in s390_iommu_iova_to_phys()
298 phys = pto[px] & ZPCI_PTE_ADDR_MASK; in s390_iommu_iova_to_phys()
/kernel/linux/linux-5.10/tools/power/pm-graph/
H A Dsleepgraph.py2551 html_tblock = '<div id="block{0}" class="tblock" style="left:{1}%;width:{2}%;"><div class="tback" style="height:{3}px"></div>\n'
2552 html_device = '<div id="{0}" title="{1}" class="thread{7}" style="left:{2}%;top:{3}px;height:{4}px;width:{5}%;{8}">{6}</div>\n'
2553 html_phase = '<div class="phase" style="left:{0}%;width:{1}%;top:{2}px;height:{3}px;background:{4}">{5}</div>\n'
2736 html_timeline = '<div id="dmesgzoombox" class="zoombox">\n<div id="{0}" class="timeline" style="height:{1}px">\n'
2759 rline = '<div class="t" style="left:0;border-left:1px solid black;border-right:0;">{0}</div>\n'
4032 .stamp {width: 100%;text-align:center;background:#888;line-height:30px;color:white;font: 25px Arial;}\n\
4033 table {width:100%;border-collapse: collapse;border:1px soli
[all...]
H A Dbootgraph.py519 html_srccall = '<div id={6} title="{5}" class="srccall" style="left:{1}%;top:{2}px;height:{3}px;width:{4}%;line-height:{3}px;">{0}</div>\n'
645 table.fstat {table-layout:fixed;padding:150px 15px 0 0;font-size:10px;column-width:30px;}\n\
646 .fstat th {width:55px;}\n\
647 .fstat td {text-align:left;width:35px;}\n\
648 .srccall {position:absolute;font-size:10px;
[all...]
/kernel/linux/linux-6.6/tools/power/pm-graph/
H A Dsleepgraph.py2739 html_tblock = '<div id="block{0}" class="tblock" style="left:{1}%;width:{2}%;"><div class="tback" style="height:{3}px"></div>\n'
2740 html_device = '<div id="{0}" title="{1}" class="thread{7}" style="left:{2}%;top:{3}px;height:{4}px;width:{5}%;{8}">{6}</div>\n'
2741 html_phase = '<div class="phase" style="left:{0}%;width:{1}%;top:{2}px;height:{3}px;background:{4}">{5}</div>\n'
2924 html_timeline = '<div id="dmesgzoombox" class="zoombox">\n<div id="{0}" class="timeline" style="height:{1}px">\n'
2947 rline = '<div class="t" style="left:0;border-left:1px solid black;border-right:0;">{0}</div>\n'
4289 .stamp {width: 100%;text-align:center;background:#888;line-height:30px;color:white;font: 25px Arial;}\n\
4290 table {width:100%;border-collapse: collapse;border:1px soli
[all...]
H A Dbootgraph.py521 html_srccall = '<div id={6} title="{5}" class="srccall" style="left:{1}%;top:{2}px;height:{3}px;width:{4}%;line-height:{3}px;">{0}</div>\n'
647 table.fstat {table-layout:fixed;padding:150px 15px 0 0;font-size:10px;column-width:30px;}\n\
648 .fstat th {width:55px;}\n\
649 .fstat td {text-align:left;width:35px;}\n\
650 .srccall {position:absolute;font-size:10px;
[all...]
/kernel/linux/linux-5.10/drivers/media/test-drivers/vivid/
H A Dvivid-kthread-cap.c635 int px; in vivid_overlay() local
645 for (px = 0; px < w; px++) { in vivid_overlay()
647 px + out_x, y, px + x)) in vivid_overlay()
649 memcpy(vbase + (px + x) * pixsize, in vivid_overlay()
650 vbuf + (px + out_x) * pixsize, in vivid_overlay()
/kernel/linux/linux-5.10/drivers/gpu/drm/imx/dcss/
H A Ddcss-dtg.c259 int px, int py, int pw, int ph) in dcss_dtg_plane_pos_set()
264 p_ulc_x = dtg->dis_ulc_x + px; in dcss_dtg_plane_pos_set()
269 if (!px && !py && !pw && !ph) { in dcss_dtg_plane_pos_set()
258 dcss_dtg_plane_pos_set(struct dcss_dtg *dtg, int ch_num, int px, int py, int pw, int ph) dcss_dtg_plane_pos_set() argument
/kernel/linux/linux-6.6/drivers/gpu/drm/amd/amdgpu/
H A Dnbio_v7_9.c399 u32 tmp, px; in nbio_v7_9_get_compute_partition_mode() local
402 px = REG_GET_FIELD(tmp, BIF_BX_PF0_PARTITION_COMPUTE_STATUS, in nbio_v7_9_get_compute_partition_mode()
405 return px; in nbio_v7_9_get_compute_partition_mode()
/kernel/linux/linux-6.6/drivers/gpu/drm/imx/dcss/
H A Ddcss-dtg.c259 int px, int py, int pw, int ph) in dcss_dtg_plane_pos_set()
264 p_ulc_x = dtg->dis_ulc_x + px; in dcss_dtg_plane_pos_set()
269 if (!px && !py && !pw && !ph) { in dcss_dtg_plane_pos_set()
258 dcss_dtg_plane_pos_set(struct dcss_dtg *dtg, int ch_num, int px, int py, int pw, int ph) dcss_dtg_plane_pos_set() argument
/kernel/linux/linux-6.6/drivers/iommu/
H A Ds390-iommu.c353 unsigned int rtx, sx, px; in s390_iommu_iova_to_phys() local
362 px = calc_px(iova); in s390_iommu_iova_to_phys()
371 pte = READ_ONCE(pto[px]); in s390_iommu_iova_to_phys()
/kernel/linux/linux-5.10/drivers/dma/
H A Dpl330.c531 struct pl330_xfer px; member
1375 struct pl330_xfer *x = &pxs->desc->px; in _setup_loops()
1396 struct pl330_xfer *x = &pxs->desc->px; in _setup_xfer()
2393 addr = desc->px.src_addr; in pl330_get_current_xferred_count()
2396 addr = desc->px.dst_addr; in pl330_get_current_xferred_count()
2631 static inline void fill_px(struct pl330_xfer *px, in fill_px() argument
2634 px->bytes = len; in fill_px()
2635 px->dst_addr = dst; in fill_px()
2636 px->src_addr = src; in fill_px()
2661 fill_px(&desc->px, ds in __pl330_prep_dma_memcpy()
[all...]
/kernel/linux/linux-6.6/drivers/dma/
H A Dpl330.c531 struct pl330_xfer px; member
1375 struct pl330_xfer *x = &pxs->desc->px; in _setup_loops()
1396 struct pl330_xfer *x = &pxs->desc->px; in _setup_xfer()
2391 addr = desc->px.src_addr; in pl330_get_current_xferred_count()
2394 addr = desc->px.dst_addr; in pl330_get_current_xferred_count()
2629 static inline void fill_px(struct pl330_xfer *px, in fill_px() argument
2632 px->bytes = len; in fill_px()
2633 px->dst_addr = dst; in fill_px()
2634 px->src_addr = src; in fill_px()
2659 fill_px(&desc->px, ds in __pl330_prep_dma_memcpy()
[all...]
/kernel/linux/linux-5.10/arch/s390/pci/
H A Dpci_dma.c102 unsigned int rtx, sx, px; in dma_walk_cpu_trans() local
114 px = calc_px(dma_addr); in dma_walk_cpu_trans()
115 return &pto[px]; in dma_walk_cpu_trans()

Completed in 32 milliseconds

123