Documented in 1 files:
Defined in 1 files as a function:
Referenced in 1 files:
Smatch caller information:
drivers/gpu/drm/panthor/panthor_pwr.c panthor_pwr_delegate_domains() -> delegate_domain()
| Type | Parameter | Key | Value |
|---|---|---|---|
| PARAM_VALUE | 0 | ptdev | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->base.anon_inode->i_mapping->host->i_sb->s_cop->inode_info_offs | 1632,1720,1808,2632,2648 |
| PARAM_VALUE | 0 | ptdev->base.dev->power.wakeirq->status | 0-4294967295 |
| PARAM_VALUE | 0 | ptdev->clks.core | 0,4096-u64max |
| PARAM_VALUE | 0 | ptdev->clks.coregroup | 0,4096-u64max |
| PARAM_VALUE | 0 | ptdev->clks.stacks | 0,4096-u64max |
| PARAM_VALUE | 0 | ptdev->devfreq | 1-u64max |
| PARAM_VALUE | 0 | ptdev->devfreq->devfreq | 0-s64max |
| PARAM_VALUE | 0 | ptdev->fw->booted | 0-1 |
| PARAM_VALUE | 0 | ptdev->gpu->pending_reqs | 0-4294967295 |
| PARAM_VALUE | 0 | ptdev->gpu_info.selected_coherency | 0,31 |
| PARAM_VALUE | 0 | ptdev->hw | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->hw->ops.l2_power_off | 1269021678885376000,7454895267167481856 |
| PARAM_VALUE | 0 | ptdev->hw->ops.l2_power_on | 4096-ptr_max |
| 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 | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->mmu_info.page_size_bitmap | 2101248 |
| PARAM_VALUE | 0 | ptdev->pm.state.counter | 0-2 |
| PARAM_VALUE | 0 | ptdev->pwr | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->scheduler->might_have_idle_groups | 0-1 |
| PARAM_VALUE | 0 | *ptdev->gpu_info.texture_features | 0-4294967295 |
| PARAM_VALUE | 1 | domain | 8 |
| BUF_SIZE | 0 | ptdev | s32min-(-1),1-s32max |
| BUF_SIZE | 0 | ptdev | s32min-(-1),1-s32max |
| DATA_SOURCE | 0 | ptdev | $0 |
| HARD_MAX | 0 | ptdev->pm.state.counter | 2 |
| 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 | 64,320-4294967104 |
| 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 |
| NO_OVERFLOW_SIMPLE | 0 | ptdev->gpu->irq.irq | |
| HALF_LOCKED2 | global &drm_unplug_srcu |
drivers/gpu/drm/panthor/panthor_pwr.c panthor_pwr_delegate_domains() -> delegate_domain()
| Type | Parameter | Key | Value |
|---|---|---|---|
| PARAM_VALUE | 0 | ptdev | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->base.anon_inode->i_mapping->host->i_sb->s_cop->inode_info_offs | 1632,1720,1808,2632,2648 |
| PARAM_VALUE | 0 | ptdev->base.dev->power.wakeirq->status | 0-4294967295 |
| PARAM_VALUE | 0 | ptdev->clks.core | 0,4096-u64max |
| PARAM_VALUE | 0 | ptdev->clks.coregroup | 0,4096-u64max |
| PARAM_VALUE | 0 | ptdev->clks.stacks | 0,4096-u64max |
| PARAM_VALUE | 0 | ptdev->devfreq | 1-u64max |
| PARAM_VALUE | 0 | ptdev->devfreq->devfreq | 0-s64max |
| PARAM_VALUE | 0 | ptdev->fw->booted | 0-1 |
| PARAM_VALUE | 0 | ptdev->gpu->pending_reqs | 0-4294967295 |
| PARAM_VALUE | 0 | ptdev->gpu_info.selected_coherency | 0,31 |
| PARAM_VALUE | 0 | ptdev->hw | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->hw->ops.l2_power_off | 1269021678885376000,7454895267167481856 |
| PARAM_VALUE | 0 | ptdev->hw->ops.l2_power_on | 4096-ptr_max |
| 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 | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->mmu_info.page_size_bitmap | 2101248 |
| PARAM_VALUE | 0 | ptdev->pm.state.counter | 0-2 |
| PARAM_VALUE | 0 | ptdev->pwr | 4096-ptr_max |
| PARAM_VALUE | 0 | ptdev->scheduler->might_have_idle_groups | 0-1 |
| PARAM_VALUE | 0 | *ptdev->gpu_info.texture_features | 0-4294967295 |
| PARAM_VALUE | 1 | domain | 1 |
| BUF_SIZE | 0 | ptdev | s32min-(-1),1-s32max |
| BUF_SIZE | 0 | ptdev | s32min-(-1),1-s32max |
| DATA_SOURCE | 0 | ptdev | $0 |
| HARD_MAX | 0 | ptdev->pm.state.counter | 2 |
| 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 | 64,320-4294967104 |
| 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 |
| NO_OVERFLOW_SIMPLE | 0 | ptdev->gpu->irq.irq | |
| HALF_LOCKED2 | global &drm_unplug_srcu |