Searched refs:vstart (Results 1 - 25 of 31) sorted by relevance

12

/linux-master/arch/arm64/include/asm/
H A Dkernel-pgtable.h46 #define SPAN_NR_ENTRIES(vstart, vend, shift) \
47 ((((vend) - 1) >> (shift)) - ((vstart) >> (shift)) + 1)
49 #define EARLY_ENTRIES(vstart, vend, shift, add) \
50 (SPAN_NR_ENTRIES(vstart, vend, shift) + (add))
52 #define EARLY_LEVEL(lvl, lvls, vstart, vend, add) \
53 (lvls > lvl ? EARLY_ENTRIES(vstart, vend, SWAPPER_BLOCK_SHIFT + lvl * (PAGE_SHIFT - 3), add) : 0)
55 #define EARLY_PAGES(lvls, vstart, vend, add) (1 /* PGDIR page */ \
56 + EARLY_LEVEL(3, (lvls), (vstart), (vend), add) /* each entry needs a next level page table */ \
57 + EARLY_LEVEL(2, (lvls), (vstart), (vend), add) /* each entry needs a next level page table */ \
58 + EARLY_LEVEL(1, (lvls), (vstart), (ven
[all...]
/linux-master/include/trace/events/
H A Dvmalloc.h15 * @vstart: a requested start range
26 unsigned long vstart, unsigned long vend, int failed),
28 TP_ARGS(addr, size, align, vstart, vend, failed),
34 __field(unsigned long, vstart)
43 __entry->vstart = vstart;
48 TP_printk("va_start: %lu size=%lu align=%lu vstart=0x%lx vend=0x%lx failed=%d",
50 __entry->vstart, __entry->vend, __entry->failed)
/linux-master/arch/riscv/include/uapi/asm/
H A Dptrace.h101 unsigned long vstart; member in struct:__riscv_v_ext_state
115 unsigned long vstart; member in struct:__riscv_v_regset_state
/linux-master/arch/powerpc/kernel/
H A Dio-workarounds.c31 unsigned long vstart, vend; local
38 vstart = (unsigned long)phb->io_base_virt;
39 vend = vstart + phb->pci_io_size - 1;
40 if ((vaddr >= vstart) && (vaddr <= vend))
/linux-master/arch/sparc/mm/
H A Dinit_64.c1685 static unsigned long __ref kernel_map_hugepud(unsigned long vstart, argument
1690 u64 pte_val = vstart;
1693 if ((vstart & mask16gb) ||
1694 (vend - vstart <= mask16gb)) {
1698 return vstart + PUD_SIZE;
1704 vend = vstart + mask16gb + 1UL;
1705 while (vstart < vend) {
1709 vstart += PUD_SIZE;
1712 return vstart;
1715 static bool kernel_can_map_hugepud(unsigned long vstart, unsigne argument
1724 kernel_map_hugepmd(unsigned long vstart, unsigned long vend, pmd_t *pmd) argument
1763 kernel_can_map_hugepmd(unsigned long vstart, unsigned long vend, bool guard) argument
1776 unsigned long vstart = PAGE_OFFSET + pstart; local
2595 vmemmap_populate(unsigned long vstart, unsigned long vend, int node, struct vmem_altmap *altmap) argument
[all...]
H A Dsrmmu.c861 unsigned long vstart = (vbase & PGDIR_MASK); local
867 if (vstart < min_vaddr || vstart >= max_vaddr)
868 return vstart;
873 while (vstart < vend) {
874 do_large_mapping(vstart, pstart);
875 vstart += PGDIR_SIZE; pstart += PGDIR_SIZE;
877 return vstart;
/linux-master/drivers/gpu/drm/msm/hdmi/
H A Dhdmi_bridge.c184 int hstart, hend, vstart, vend; local
194 vstart = mode->vtotal - mode->vsync_start - 1;
197 DBG("htotal=%d, vtotal=%d, hstart=%d, hend=%d, vstart=%d, vend=%d",
198 mode->htotal, mode->vtotal, hstart, hend, vstart, vend);
208 HDMI_ACTIVE_VSYNC_START(vstart) |
215 HDMI_VSYNC_ACTIVE_F2_START(vstart + 1) |
/linux-master/drivers/staging/sm750fb/
H A Dsm750_cursor.c102 pstart = cursor->vstart;
152 pstart = cursor->vstart;
H A Dsm750.h128 char __iomem *vstart; member in struct:lynx_cursor
H A Dsm750.c454 memset_io(cursor->vstart, 0x0, cursor->size);
466 memset_io(cursor->vstart, 0x0, cursor->size);
767 crtc->cursor.vstart = sm750_dev->pvMem + crtc->cursor.offset;
769 memset_io(crtc->cursor.vstart, 0, crtc->cursor.size);
/linux-master/arch/riscv/kernel/
H A Dptrace.c108 ptrace_vstate.vstart = vstate->vstart;
142 vstate->vstart = ptrace_vstate.vstart;
/linux-master/arch/alpha/boot/
H A Dbootpz.c76 check_range(unsigned long vstart, unsigned long vend, argument
83 vstart, vend, kstart, kend);
86 for (vaddr = vstart; vaddr <= vend; vaddr += PAGE_SIZE)
/linux-master/drivers/scsi/csiostor/
H A Dcsio_wr.c119 __be64 *d = (__be64 *)(flq->vstart);
236 q->vstart = dma_alloc_coherent(&hw->pdev->dev, qsz, &q->pstart,
238 if (!q->vstart) {
262 q->vwrap = (void *)((uintptr_t)(q->vstart) + qsz
316 q->vwrap = (void *)((uintptr_t)(q->vstart) + qsz
321 q->vwrap = (void *)((uintptr_t)(q->vstart) + qsz
775 wr = (void *)((uintptr_t)q->vstart +
868 void *cwr = (void *)((uintptr_t)(q->vstart) +
912 wrp->addr2 = q->vstart;
1135 void *wr = (void *)((uintptr_t)q->vstart
[all...]
H A Dcsio_wr.h401 void *vstart; /* Base virtual address member in struct:csio_q
457 #define csio_q_vstart(__hw, __idx) ((__hw)->wrm.q_arr[(__idx)]->vstart)
/linux-master/drivers/gpu/drm/i915/display/
H A Ddvo_ns2501.c214 u16 vstart; /* vertical start, registers C5/C6 */ member in struct:ns2501_configuration
241 .vstart = 22,
261 .vstart = 26,
280 .vstart = 15,
621 ns2501_writeb(dvo, NS2501_REGC5, conf->vstart & 0xff);
622 ns2501_writeb(dvo, NS2501_REGC6, conf->vstart >> 8);
/linux-master/mm/
H A Dvmalloc.c1459 unsigned long align, unsigned long vstart)
1463 if (va->va_start > vstart)
1466 nva_start_addr = ALIGN(vstart, align);
1470 nva_start_addr < vstart)
1485 unsigned long align, unsigned long vstart, bool adjust_search_size)
1501 vstart < va->va_start) {
1504 if (is_within_this_va(va, size, align, vstart))
1520 * due to "vstart" restriction or an alignment overhead
1525 if (is_within_this_va(va, size, align, vstart))
1529 vstart <
1458 is_within_this_va(struct vmap_area *va, unsigned long size, unsigned long align, unsigned long vstart) argument
1484 find_vmap_lowest_match(struct rb_root *root, unsigned long size, unsigned long align, unsigned long vstart, bool adjust_search_size) argument
1551 find_vmap_lowest_linear_match(struct list_head *head, unsigned long size, unsigned long align, unsigned long vstart) argument
1571 unsigned long vstart; local
1721 va_alloc(struct vmap_area *va, struct rb_root *root, struct list_head *head, unsigned long size, unsigned long align, unsigned long vstart, unsigned long vend) argument
1751 __alloc_vmap_area(struct rb_root *root, struct list_head *head, unsigned long size, unsigned long align, unsigned long vstart, unsigned long vend) argument
1860 node_pool_del_va(struct vmap_node *vn, unsigned long size, unsigned long align, unsigned long vstart, unsigned long vend) argument
1902 node_alloc(unsigned long size, unsigned long align, unsigned long vstart, unsigned long vend, unsigned long *addr, unsigned int *vn_id) argument
1933 alloc_vmap_area(unsigned long size, unsigned long align, unsigned long vstart, unsigned long vend, int node, gfp_t gfp_mask, unsigned long va_flags) argument
[all...]
/linux-master/drivers/media/usb/gspca/
H A Dsn9c20x.c101 u8 vstart; member in struct:sd
686 0x10, 0x61 and sd->hstart, vstart = 3, fixes ugly colored borders */
1103 sd->vstart = 7;
1117 sd->vstart = 2;
1131 sd->vstart = 11;
1144 sd->vstart = 3;
1158 sd->vstart = 1;
1176 sd->vstart = 2;
1194 sd->vstart = 2;
1217 sd->vstart
[all...]
/linux-master/arch/riscv/kvm/
H A Dvcpu_vector.c107 case KVM_REG_RISCV_VECTOR_CSR_REG(vstart):
108 *reg_addr = &cntx->vector.vstart;
/linux-master/arch/riscv/include/asm/
H A Dvector.h86 : "=r" (dest->vstart), "=r" (dest->vtype), "=r" (dest->vl),
99 : : "r" (src->vstart), "r" (src->vtype), "r" (src->vl),
/linux-master/arch/x86/xen/
H A Dmmu_pv.c2328 unsigned long vstart = (unsigned long)phys_to_virt(pstart); local
2333 memset((void *) vstart, 0, PAGE_SIZE << order);
2338 xen_zap_pfn_range(vstart, order, in_frames, NULL);
2341 out_frame = virt_to_pfn((void *)vstart);
2348 xen_remap_exchanged_ptes(vstart, order, NULL, out_frame);
2350 xen_remap_exchanged_ptes(vstart, order, in_frames, 0);
2354 *dma_handle = virt_to_machine(vstart).maddr;
2363 unsigned long vstart; local
2368 vstart = (unsigned long)phys_to_virt(pstart);
2369 memset((void *) vstart,
[all...]
/linux-master/kernel/dma/
H A Dswiotlb.c436 unsigned char *vstart = NULL; local
468 vstart = (void *)__get_free_pages(gfp_mask | __GFP_NOWARN,
470 if (vstart)
477 if (!vstart)
481 rc = remap(vstart, nslabs);
483 free_pages((unsigned long)vstart, order);
509 set_memory_decrypted((unsigned long)vstart,
511 swiotlb_init_io_tlb_pool(mem, virt_to_phys(vstart), nslabs, true,
521 free_pages((unsigned long)vstart, order);
/linux-master/drivers/media/i2c/
H A Dov7670.c196 int vstart; /* sense to humans, but evidently the sensor */ member in struct:ov7670_win_size
731 .vstart = 10,
742 .vstart = 14,
753 .vstart = 12,
764 .vstart = 14,
782 .vstart = 14, /* Empirically determined */
916 int vstart, int vstop)
940 ret = ov7670_write(sd, REG_VSTART, (vstart >> 2) & 0xff);
949 v = (v & 0xf0) | ((vstop & 0x3) << 2) | (vstart & 0x3);
1069 ret = ov7670_set_hw(sd, wsize->hstart, wsize->hstop, wsize->vstart,
915 ov7670_set_hw(struct v4l2_subdev *sd, int hstart, int hstop, int vstart, int vstop) argument
[all...]
H A Dmt9v011.c272 unsigned vstart, hstart; local
290 vstart = 8 + (480 - core->height) / 2;
291 mt9v011_write(sd, R01_MT9V011_ROWSTART, vstart);
/linux-master/arch/powerpc/include/asm/book3s/64/
H A Dmmu-hash.h495 extern int htab_bolt_mapping(unsigned long vstart, unsigned long vend,
498 int htab_remove_mapping(unsigned long vstart, unsigned long vend,
/linux-master/arch/powerpc/mm/book3s64/
H A Dhash_utils.c354 int htab_bolt_mapping(unsigned long vstart, unsigned long vend, argument
368 vstart, vend, pstart, prot, psize, ssize);
371 vaddr = ALIGN(vstart, step);
441 int htab_remove_mapping(unsigned long vstart, unsigned long vend, argument
456 vaddr = ALIGN_DOWN(vstart, step);

Completed in 305 milliseconds

12