/linux-master/arch/arm64/include/asm/ |
H A D | kernel-pgtable.h | 46 #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 D | vmalloc.h | 15 * @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 D | ptrace.h | 101 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 D | io-workarounds.c | 31 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 D | init_64.c | 1685 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 D | srmmu.c | 861 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 D | hdmi_bridge.c | 184 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 D | sm750_cursor.c | 102 pstart = cursor->vstart; 152 pstart = cursor->vstart;
|
H A D | sm750.h | 128 char __iomem *vstart; member in struct:lynx_cursor
|
H A D | sm750.c | 454 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 D | ptrace.c | 108 ptrace_vstate.vstart = vstate->vstart; 142 vstate->vstart = ptrace_vstate.vstart;
|
/linux-master/arch/alpha/boot/ |
H A D | bootpz.c | 76 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 D | csio_wr.c | 119 __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 D | csio_wr.h | 401 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 D | dvo_ns2501.c | 214 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 D | vmalloc.c | 1459 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 D | sn9c20x.c | 101 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 D | vcpu_vector.c | 107 case KVM_REG_RISCV_VECTOR_CSR_REG(vstart): 108 *reg_addr = &cntx->vector.vstart;
|
/linux-master/arch/riscv/include/asm/ |
H A D | vector.h | 86 : "=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 D | mmu_pv.c | 2328 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 D | swiotlb.c | 436 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 D | ov7670.c | 196 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 D | mt9v011.c | 272 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 D | mmu-hash.h | 495 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 D | hash_utils.c | 354 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);
|