Open Menu /

Documented in 1 files:

Defined in 1 files as a prototype:

Defined in 1 files as a function:

Referenced in 1 files:

Smatch caller information:

drivers/gpu/drm/panthor/panthor_device.c panthor_device_init() -> panthor_gpu_init()

Type Parameter Key Value
PARAM_VALUE 0 ptdev 4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev 4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev->bus 0,4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev->class 0,4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev->devres_head.prev 4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev->devres_head.prev->next 4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev->devres_head.prev->next->next 4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev->dma_mem->pfn_base 0-s64max
PARAM_VALUE 0 ptdev->base.dev->power.last_status (-1)
PARAM_VALUE 0 ptdev->base.dev->power.qos 1-ptr_max
PARAM_VALUE 0 ptdev->base.dev->power.qos->freq.max_freq.default_value s32max
PARAM_VALUE 0 ptdev->base.dev->power.qos->freq.max_freq.no_constraint_value s32max
PARAM_VALUE 0 ptdev->base.dev->power.qos->freq.max_freq.target_value s32max
PARAM_VALUE 0 ptdev->base.dev->power.qos->freq.max_freq.type 2
PARAM_VALUE 0 ptdev->base.dev->power.qos->latency_tolerance.no_constraint_value (-1)
PARAM_VALUE 0 ptdev->base.dev->power.qos->latency_tolerance.type 2
PARAM_VALUE 0 ptdev->base.dev->power.request 0-4
PARAM_VALUE 0 ptdev->base.dev->power.runtime_error s32min-(-17),(-15)-(-14),(-12),(-10)-s32max
PARAM_VALUE 0 ptdev->base.dev->power.wakeirq 0,4096-ptr_max
PARAM_VALUE 0 ptdev->base.dev->power.wakeirq->status 0-4294967295
PARAM_VALUE 0 ptdev->base.dev->type 0,4096-ptr_max
PARAM_VALUE 0 ptdev->base.managed.resources.next 4096-ptr_max
PARAM_VALUE 0 ptdev->base.managed.resources.next->next 4096-ptr_max
PARAM_VALUE 0 ptdev->base.managed.resources.next->prev 4096-ptr_max
PARAM_VALUE 0 ptdev->clks.core 0,4096-ptr_max
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.deferred_resume 0-1
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.idle_notification 0-1
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.request 0-4294967295
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.request_pending 0-1
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.runtime_error s32min-s32max
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.runtime_status s32min-s32max
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.timer_autosuspends 0-1
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.usage_count.counter s32min-s32max
PARAM_VALUE 0 ptdev->clks.core->core->dev->power.wakeirq->status 0-4294967295
PARAM_VALUE 0 ptdev->clks.coregroup 0,4096-ptr_max
PARAM_VALUE 0 ptdev->clks.stacks 0,4096-ptr_max
PARAM_VALUE 0 ptdev->devfreq 4096-ptr_max
PARAM_VALUE 0 ptdev->gems.lock.dep_map->name 0-255
PARAM_VALUE 0 ptdev->gems.lock.first_waiter 0
PARAM_VALUE 0 ptdev->gems.lock.magic 4096-ptr_max
PARAM_VALUE 0 ptdev->gems.lock.osq.tail.counter 0
PARAM_VALUE 0 ptdev->gems.lock.owner.counter 0
PARAM_VALUE 0 ptdev->gems.node.next 4096-ptr_max
PARAM_VALUE 0 ptdev->gems.node.next->next 4096-ptr_max
PARAM_VALUE 0 ptdev->gems.node.prev 4096-ptr_max
PARAM_VALUE 0 ptdev->gems.node.prev->next 4096-ptr_max
PARAM_VALUE 0 ptdev->gems.node.prev->prev 4096-ptr_max
PARAM_VALUE 0 ptdev->gpu_info.gpu_id 1-u32max
PARAM_VALUE 0 ptdev->hw 5872954781401980928,6281872025581350912
PARAM_VALUE 0 ptdev->hw->ops.l2_power_off 1269021678885376000,7454895267167481856
PARAM_VALUE 0 ptdev->hw->ops.l2_power_on 344593156557139968,8847262122250321920
PARAM_VALUE 0 ptdev->hw->ops.power_changed_off 0,1856157486973640704
PARAM_VALUE 0 ptdev->hw->ops.power_changed_on 0,2775241924151676928
PARAM_VALUE 0 ptdev->hw->ops.soft_reset 3077085170874974208,8766734615931842560
PARAM_VALUE 0 ptdev->iomem 4096-ptr_max
PARAM_VALUE 0 ptdev->pm.dummy_latest_flush 4096-ptr_max
PARAM_VALUE 0 ptdev->pm.dummy_latest_flush->_refcount.counter 1
PARAM_VALUE 0 ptdev->pm.mmio_lock.dep_map->name 0-255
PARAM_VALUE 0 ptdev->pm.mmio_lock.first_waiter 0
PARAM_VALUE 0 ptdev->pm.mmio_lock.magic 4096-ptr_max
PARAM_VALUE 0 ptdev->pm.mmio_lock.osq.tail.counter 0
PARAM_VALUE 0 ptdev->pm.mmio_lock.owner.counter 0
PARAM_VALUE 0 ptdev->pm.state.counter 0
PARAM_VALUE 0 ptdev->reset.wq 4096-ptr_max
PARAM_VALUE 0 ptdev->unplug.done.done 0
PARAM_VALUE 0 ptdev->unplug.done.wait.lock.magic 3735899821
PARAM_VALUE 0 ptdev->unplug.done.wait.lock.owner (-1)
PARAM_VALUE 0 ptdev->unplug.done.wait.lock.owner_cpu u32max
PARAM_VALUE 0 ptdev->unplug.done.wait.task_list.next 4096-ptr_max
PARAM_VALUE 0 ptdev->unplug.done.wait.task_list.next->next 4096-ptr_max
PARAM_VALUE 0 ptdev->unplug.done.wait.task_list.prev 4096-ptr_max
PARAM_VALUE 0 ptdev->unplug.done.wait.task_list.prev->next 4096-ptr_max
PARAM_VALUE 0 ptdev->unplug.done.wait.task_list.prev->prev 4096-ptr_max
PARAM_VALUE 0 ptdev->unplug.lock.dep_map->name 0-255
PARAM_VALUE 0 ptdev->unplug.lock.first_waiter 0
PARAM_VALUE 0 ptdev->unplug.lock.magic 4096-ptr_max
PARAM_VALUE 0 ptdev->unplug.lock.osq.tail.counter 0
PARAM_VALUE 0 ptdev->unplug.lock.owner.counter 0
PARAM_VALUE 0 *ptdev->gpu_info.texture_features 0-4294967295
BUF_SIZE 0 ptdev->reset.wq (-1),512,528-8720
CAPPED_DATA 0 ptdev->base.dev 1
DATA_SOURCE 0 ptdev $0
RX_PATH
TASK_NOT_RUNNING
HOST_DATA 0 ptdev->gpu_info.as_present 0-u32max
HOST_DATA 0 ptdev->gpu_info.coherency_features 0-u32max
HOST_DATA 0 ptdev->gpu_info.core_features 0-u32max
HOST_DATA 0 ptdev->gpu_info.csf_id 0-u32max
HOST_DATA 0 ptdev->gpu_info.gpu_rev 0-u32max
HOST_DATA 0 ptdev->gpu_info.l2_features 0-u32max
HOST_DATA 0 ptdev->gpu_info.max_threads 0-u32max
HOST_DATA 0 ptdev->gpu_info.mem_features 0-u32max
HOST_DATA 0 ptdev->gpu_info.mmu_features 0-u32max
HOST_DATA 0 ptdev->gpu_info.thread_features 0-u32max
HOST_DATA 0 ptdev->gpu_info.thread_max_barrier_size 0-u32max
HOST_DATA 0 ptdev->gpu_info.thread_max_workgroup_size 0-u32max
HOST_DATA 0 ptdev->gpu_info.tiler_features 0-u32max