Open Menu /

Documented in 1 files:

Defined in 1 files as a prototype:

Defined in 1 files as a function:

Referenced in 2 files:

Smatch caller information:

drivers/gpu/drm/panthor/panthor_sched.c group_bind_locked() -> panthor_vm_active()

Type Parameter Key Value
LOCK2 &sched->lock
LOCK2 global &drm_unplug_srcu
HALF_LOCKED2 &pool->lock
TYPE_LOCK (struct panthor_scheduler)->lock

drivers/gpu/drm/panthor/panthor_fw.c panthor_fw_init() -> panthor_vm_active()

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->base.bo_defer.first 0
PARAM_VALUE 0 vm->base.flags 3
PARAM_VALUE 0 vm->base.kernel_alloc_node.flags 0
PARAM_VALUE 0 vm->base.kernel_alloc_node.gem.obj 0
PARAM_VALUE 0 vm->base.kernel_alloc_node.vm_bo 0
PARAM_VALUE 0 vm->base.kref.refcount.refs.counter 1
PARAM_VALUE 0 vm->base.mm_start 0
PARAM_VALUE 0 vm->base.ops 8339243441545060352
PARAM_VALUE 0 vm->base.ops->op_alloc 0,4178244968145121280
PARAM_VALUE 0 vm->base.ops->sm_step_map 0,912682263357759488,3850699923445227520,8379760394559614976,8609383518014025728
PARAM_VALUE 0 vm->base.ops->sm_step_remap 0,3850699923445227520,5121074557911261184,5420759306209017856,8609383518014025728
PARAM_VALUE 0 vm->base.ops->sm_step_unmap 0,3850699923445227520,5914183354706407424,7504656685248028672,8609383518014025728
PARAM_VALUE 0 vm->base.ops->vm_bo_free 0,5555473383884926976
PARAM_VALUE 0 vm->base.ops->vm_bo_validate 0,248747483245506560,265657736556892160,1638191084720013312,1986338527227244544
PARAM_VALUE 0 vm->base.ops->vm_free 0,826467068035764224,3805946052293255168,5326365468746117120,6598819279086505984
PARAM_VALUE 0 vm->base.r_obj->_resv.lock.ww_class 8825623990767841280
PARAM_VALUE 0 vm->base.r_obj->funcs 1406244332369195008
PARAM_VALUE 0 vm->base.r_obj->refcount.refcount.refs.counter 1
PARAM_VALUE 0 vm->base.r_obj->vma_node.vm_lock.magic 3736018669
PARAM_VALUE 0 vm->base.r_obj->vma_node.vm_lock.owner (-1)
PARAM_VALUE 0 vm->base.r_obj->vma_node.vm_lock.owner_cpu 4294967295
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 4294967295
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 4294967295
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.tail.counter s64min-(-4096),4096-s64max
PARAM_VALUE 0 vm->entity.last_scheduled 0
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.stats->kref.refcount.refs.counter 1
PARAM_VALUE 0 vm->entity.stopped 0
PARAM_VALUE 0 vm->for_mcu 1
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.osq.tail.counter 0
PARAM_VALUE 0 vm->heaps.lock.owner.counter 0
PARAM_VALUE 0 vm->kernel_auto_va.start 67108864
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.rb_hole_size.__rb_parent_color 1
PARAM_VALUE 0 vm->mm.head_node.subtree_max_hole 1
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.osq.tail.counter 0
PARAM_VALUE 0 vm->mm_lock.owner.counter 0
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.osq.tail.counter 0
PARAM_VALUE 0 vm->op_lock.owner.counter 0
PARAM_VALUE 0 vm->ptdev 4096-ptr_max
PARAM_VALUE 0 vm->ptdev->clks.core s64min-(-4096),0,4096-s64max
PARAM_VALUE 0 vm->ptdev->clks.coregroup s64min-(-4096),0,4096-s64max
PARAM_VALUE 0 vm->ptdev->clks.stacks s64min-(-4096),0,4096-s64max
PARAM_VALUE 0 vm->ptdev->devfreq s64min-(-4096),4096-s64max
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 s64min-(-4096),4096-s64max
PARAM_VALUE 0 vm->ptdev->mmu_info.page_size_bitmap 2101248
PARAM_VALUE 0 vm->reclaim.lru.count 0
PARAM_VALUE 0 vm->root_page_table 0,s64max
PARAM_VALUE 0 vm->sched._score.counter 0
PARAM_VALUE 0 vm->sched.avg_job_us.internal 0
PARAM_VALUE 0 vm->sched.credit_limit 1
PARAM_VALUE 0 vm->sched.dev s64min-(-4096),4096-s64max
PARAM_VALUE 0 vm->sched.hang_limit 0
PARAM_VALUE 0 vm->sched.job_id_count.counter 0
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->prepare_job 0,6347586488842227712
PARAM_VALUE 0 vm->sched.ready 1
PARAM_VALUE 0 vm->sched.rq.head_prio (-1)
PARAM_VALUE 0 vm->sched.timeout s64max
PARAM_VALUE 0 vm->user_va_range 0
BUF_SIZE 0 vm 2384
BUF_SIZE 0 vm 2384
DATA_SOURCE 0 vm r panthor_vm_create
TERMINATED 0 vm->sched.name 1
RX_PATH
TASK_NOT_RUNNING
HOST_DATA 0 vm->base.mm_range 1[c]
HOST_DATA 0 vm->mm.head_node.size s64min-s64max
HOST_DATA 0 vm->ptdev->gpu_info.as_present 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.coherency_features 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.core_features 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.csf_id 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.gpu_rev 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.l2_features 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.max_threads 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.mem_features 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.mmu_features 64,320-4294967104
HOST_DATA 0 vm->ptdev->gpu_info.thread_features 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.thread_max_barrier_size 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.thread_max_workgroup_size 0-4294967295
HOST_DATA 0 vm->ptdev->gpu_info.tiler_features 0-4294967295

drivers/gpu/drm/panthor/panthor_fw.c panthor_fw_post_reset() -> panthor_vm_active()

Type Parameter Key Value
LOCK2 global &drm_unplug_srcu