| PARAM_VALUE |
0 |
ptdev |
4096-ptr_max |
| PARAM_VALUE |
0 |
ptdev->base.anon_inode->i_mapping->host->i_sb->s_cop->empty_dir |
0,86,661756434209751040,4392966320616476672,5234023279986843648,8614756098313990144 |
| PARAM_VALUE |
0 |
ptdev->base.anon_inode->i_mapping->host->i_sb->s_cop->get_context |
0,706,17350455714160640,4513809449498124288,5149251875611672576,7067778626864828416 |
| PARAM_VALUE |
0 |
ptdev->base.anon_inode->i_mapping->host->i_sb->s_cop->set_context |
0,67,317457138841939968,3250154607523569664,5979066299606671360,6756104566897242112 |
| PARAM_VALUE |
0 |
ptdev->base.anon_inode->i_mapping->host->i_sb->s_export_op->encode_fh |
0,2,1398972869330624512,1616549510479982592,2037984473558433792,2776440803454029824,3228746867770966016,3502492669594062848,3526768263295340544,3559173554394271744,5000850239487131648,5583386343686406144,5817357685191483392-s64max |
| 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 |
4096-ptr_max |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->csif_info.cs_reg_count |
1-256 |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->csif_info.csg_slot_count |
0-16 |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->csif_info.scoreboard_slot_count |
0-255 |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->csif_info.unpreserved_cs_reg_count |
4 |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->gpu_info.selected_coherency |
0,31 |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->hw |
5872954781401980928,6281872025581350912 |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->mmu_info.page_size_bitmap |
2101248 |
| PARAM_VALUE |
0 |
ptdev->gpu->irq.ptdev->profile_mask |
0-2 |
| 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->pending_reqs |
0-4294967295 |
| PARAM_VALUE |
0 |
ptdev->scheduler->might_have_idle_groups |
0-1 |
| PARAM_VALUE |
0 |
*ptdev->gpu_info.texture_features |
0-4294967295 |
| 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 |
|
|
|
| NOCHECK_CALL |
|
|
|
| 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 |
|