panthor_vm_stop identifier - Linux source code next-20260811

Projects

linux

Versions

FIXME
- FIXME
  - next-20260811

Defined in 1 files as a function:

drivers/gpu/drm/panthor/panthor_mmu.c, line 869 (as a function)

Referenced in 1 files:

drivers/gpu/drm/panthor/panthor_mmu.c
- line 1991
- line 2946

Smatch caller information:

drivers/gpu/drm/panthor/panthor_mmu.c panthor_mmu_pre_reset() -> panthor_vm_stop()

Type	Parameter	Key	Value
PARAM_VALUE	0	vm	4096-ptr_max
CAPPED_DATA	0	&vm->node	1
NOCHECK_CALL
LOCK2		&ptdev->mmu->vm.lock
LOCK2		global &drm_unplug_srcu
HALF_LOCKED2		&pool->lock
TYPE_LOCK		(struct panthor_mmu)->vm.lock

drivers/gpu/drm/panthor/panthor_mmu.c panthor_vm_create() -> panthor_vm_stop()

Type	Parameter	Key	Value
PARAM_VALUE	0	vm	4096-ptr_max
PARAM_VALUE	0	vm->as.active_cnt.refs.counter	0
PARAM_VALUE	0	vm->as.id	(-1)
PARAM_VALUE	0	vm->as.lru_node.next	4096-ptr_max
PARAM_VALUE	0	vm->as.lru_node.next->next	4096-ptr_max
PARAM_VALUE	0	vm->as.lru_node.prev	4096-ptr_max
PARAM_VALUE	0	vm->as.lru_node.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->as.lru_node.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->entity.cb.func	0
PARAM_VALUE	0	vm->entity.cb.node.next	0
PARAM_VALUE	0	vm->entity.cb.node.prev	0
PARAM_VALUE	0	vm->entity.dependency	0
PARAM_VALUE	0	vm->entity.entity_idle.done	u32max
PARAM_VALUE	0	vm->entity.entity_idle.wait.lock.dep_map->name	0-255
PARAM_VALUE	0	vm->entity.entity_idle.wait.lock.owner	(-1)
PARAM_VALUE	0	vm->entity.entity_idle.wait.lock.owner_cpu	u32max
PARAM_VALUE	0	vm->entity.entity_idle.wait.task_list.next	4096-ptr_max
PARAM_VALUE	0	vm->entity.entity_idle.wait.task_list.next->next	4096-ptr_max
PARAM_VALUE	0	vm->entity.entity_idle.wait.task_list.prev	4096-ptr_max
PARAM_VALUE	0	vm->entity.entity_idle.wait.task_list.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->entity.entity_idle.wait.task_list.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->entity.fence_seq.counter	0
PARAM_VALUE	0	vm->entity.guilty	0
PARAM_VALUE	0	vm->entity.job_queue.head	0
PARAM_VALUE	0	vm->entity.job_queue.job_count.counter	0
PARAM_VALUE	0	vm->entity.job_queue.tail.counter	s64min-(-4096),4096-s64max
PARAM_VALUE	0	vm->entity.last_scheduled	0
PARAM_VALUE	0	vm->entity.list.next	4096-ptr_max
PARAM_VALUE	0	vm->entity.list.next->next	4096-ptr_max
PARAM_VALUE	0	vm->entity.list.prev	4096-ptr_max
PARAM_VALUE	0	vm->entity.list.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->entity.list.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->entity.num_sched_list	1
PARAM_VALUE	0	vm->entity.oldest_job_waiting	0
PARAM_VALUE	0	vm->entity.rb_tree_node.rb_left	0
PARAM_VALUE	0	vm->entity.rb_tree_node.rb_right	0
PARAM_VALUE	0	vm->entity.rq	4096-ptr_max
PARAM_VALUE	0	vm->entity.sched_list	0,4096-ptr_max
PARAM_VALUE	0	vm->entity.stats	4096-ptr_max
PARAM_VALUE	0	vm->entity.stats->avg_job_us.internal	0
PARAM_VALUE	0	vm->entity.stats->kref.refcount.refs.counter	1
PARAM_VALUE	0	vm->entity.stopped	0
PARAM_VALUE	0	vm->heaps.lock.dep_map->name	0-255
PARAM_VALUE	0	vm->heaps.lock.first_waiter	0
PARAM_VALUE	0	vm->heaps.lock.magic	4096-ptr_max
PARAM_VALUE	0	vm->heaps.lock.osq.tail.counter	0
PARAM_VALUE	0	vm->heaps.lock.owner.counter	0
PARAM_VALUE	0	vm->mm.color_adjust	0
PARAM_VALUE	0	vm->mm.head_node.flags	0
PARAM_VALUE	0	vm->mm.head_node.hole_size	1
PARAM_VALUE	0	vm->mm.head_node.hole_stack.next	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.hole_stack.prev	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->color_adjust	0
PARAM_VALUE	0	vm->mm.head_node.mm->head_node.flags	0
PARAM_VALUE	0	vm->mm.head_node.mm->head_node.mm	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->hole_stack.next	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->hole_stack.next->next	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->hole_stack.next->prev	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->hole_stack.prev	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->holes_addr.rb_node	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->holes_size.rb_leftmost	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.mm->holes_size.rb_root.rb_node	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.node_list.next	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.node_list.next->next	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.node_list.prev	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.node_list.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.node_list.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.rb_hole_addr.rb_left	0,4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.rb_hole_addr.rb_right	0,4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.rb_hole_size.__rb_parent_color	1
PARAM_VALUE	0	vm->mm.head_node.rb_hole_size.rb_left	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.rb_hole_size.rb_right	4096-ptr_max
PARAM_VALUE	0	vm->mm.head_node.start	1-u64max
PARAM_VALUE	0	vm->mm.head_node.subtree_max_hole	1
PARAM_VALUE	0	vm->mm.hole_stack.next	4096-ptr_max
PARAM_VALUE	0	vm->mm.hole_stack.next->next	4096-ptr_max
PARAM_VALUE	0	vm->mm.hole_stack.prev	4096-ptr_max
PARAM_VALUE	0	vm->mm.hole_stack.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->mm.hole_stack.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->mm.scan_active	0
PARAM_VALUE	0	vm->mm_lock.dep_map->name	0-255
PARAM_VALUE	0	vm->mm_lock.first_waiter	0
PARAM_VALUE	0	vm->mm_lock.magic	4096-ptr_max
PARAM_VALUE	0	vm->mm_lock.osq.tail.counter	0
PARAM_VALUE	0	vm->mm_lock.owner.counter	0
PARAM_VALUE	0	vm->node.next	4096-ptr_max
PARAM_VALUE	0	vm->node.next->next	4096-ptr_max
PARAM_VALUE	0	vm->node.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->node.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->op_lock.dep_map->name	0-255
PARAM_VALUE	0	vm->op_lock.first_waiter	0
PARAM_VALUE	0	vm->op_lock.magic	4096-ptr_max
PARAM_VALUE	0	vm->op_lock.osq.tail.counter	0
PARAM_VALUE	0	vm->op_lock.owner.counter	0
PARAM_VALUE	0	vm->pgtbl_ops	4096-ptr_max
PARAM_VALUE	0	vm->ptdev	4096-ptr_max
PARAM_VALUE	0	vm->ptdev->clks.core	0,4096-u64max
PARAM_VALUE	0	vm->ptdev->clks.coregroup	0,4096-u64max
PARAM_VALUE	0	vm->ptdev->clks.stacks	0,4096-u64max
PARAM_VALUE	0	vm->ptdev->devfreq	1-u64max
PARAM_VALUE	0	vm->ptdev->gpu_info.selected_coherency	0,31
PARAM_VALUE	0	vm->ptdev->hw	5872954781401980928,6281872025581350912
PARAM_VALUE	0	vm->ptdev->mmu	4096-ptr_max
PARAM_VALUE	0	vm->ptdev->mmu_info.page_size_bitmap	2101248
PARAM_VALUE	0	vm->reclaim.lru.count	0
PARAM_VALUE	0	vm->reclaim.lru.list.next	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru.list.next->next	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru.list.prev	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru.list.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru.list.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru_node.next	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru_node.next->next	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru_node.prev	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru_node.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->reclaim.lru_node.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->root_page_table	0,9223372036854775807
PARAM_VALUE	0	vm->sched._score.counter	0
PARAM_VALUE	0	vm->sched.avg_job_us.internal	0
PARAM_VALUE	0	vm->sched.credit_count.counter	0
PARAM_VALUE	0	vm->sched.credit_limit	1
PARAM_VALUE	0	vm->sched.hang_limit	0
PARAM_VALUE	0	vm->sched.job_id_count.counter	0
PARAM_VALUE	0	vm->sched.job_scheduled.head.next	4096-ptr_max
PARAM_VALUE	0	vm->sched.job_scheduled.head.next->next	4096-ptr_max
PARAM_VALUE	0	vm->sched.job_scheduled.head.prev	4096-ptr_max
PARAM_VALUE	0	vm->sched.job_scheduled.head.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->sched.job_scheduled.head.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->sched.name	4930682689402630144
PARAM_VALUE	0	vm->sched.ops	6137717106612879360
PARAM_VALUE	0	vm->sched.ops->cancel_job	0,7588619251115601920
PARAM_VALUE	0	vm->sched.ops->free_job	4096-ptr_max
PARAM_VALUE	0	vm->sched.ops->prepare_job	0,6347586488842227712
PARAM_VALUE	0	vm->sched.ops->run_job	4096-ptr_max
PARAM_VALUE	0	vm->sched.ops->timedout_job	0,4096-ptr_max
PARAM_VALUE	0	vm->sched.pause_submit	0
PARAM_VALUE	0	vm->sched.pending_list.next	4096-ptr_max
PARAM_VALUE	0	vm->sched.pending_list.next->next	4096-ptr_max
PARAM_VALUE	0	vm->sched.pending_list.prev	4096-ptr_max
PARAM_VALUE	0	vm->sched.pending_list.prev->next	4096-ptr_max
PARAM_VALUE	0	vm->sched.pending_list.prev->prev	4096-ptr_max
PARAM_VALUE	0	vm->sched.ready	1
PARAM_VALUE	0	vm->sched.rq.head_prio	(-1)
PARAM_VALUE	0	vm->sched.score	1-u64max
PARAM_VALUE	0	vm->sched.submit_wq	1-u64max
PARAM_VALUE	0	vm->sched.timeout	s64max
PARAM_VALUE	0	vm->user_va_range	0-18446744073709551614
BUF_SIZE	0	vm	2304
BUF_SIZE	0	vm->pgtbl_ops	40
DATA_SOURCE	0	vm	r _kzalloc_noprof
STR_LEN	0	vm->sched.name	(-1)
TERMINATED	0	vm->sched.name	1
MEM_ZERO	0	&vm->entity
RX_PATH
TASK_NOT_RUNNING
NOCHECK_CALL
HOST_DATA	0	vm->mm.head_node.size	0-u64max
HOST_DATA	0	vm->ptdev->gpu_info.as_present	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.coherency_features	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.core_features	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.csf_id	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.gpu_rev	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.l2_features	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.max_threads	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.mem_features	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.mmu_features	64,320-4294967104
HOST_DATA	0	vm->ptdev->gpu_info.thread_features	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.thread_max_barrier_size	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.thread_max_workgroup_size	0-u32max
HOST_DATA	0	vm->ptdev->gpu_info.tiler_features	0-u32max
LOCK2		&ptdev->mmu->vm.lock
HALF_LOCKED2		global &drm_unplug_srcu
TYPE_LOCK		(struct panthor_mmu)->vm.lock