Changeset View
Changeset View
Standalone View
Standalone View
intern/cycles/kernel/device/metal/compat.h
| Show First 20 Lines • Show All 111 Lines • ▼ Show 20 Lines | void run(thread MetalKernelContext& context, \ | ||||
| const uint metal_global_id, \ | const uint metal_global_id, \ | ||||
| const ushort metal_local_id, \ | const ushort metal_local_id, \ | ||||
| const ushort metal_local_size, \ | const ushort metal_local_size, \ | ||||
| uint simdgroup_size, \ | uint simdgroup_size, \ | ||||
| uint simd_lane_index, \ | uint simd_lane_index, \ | ||||
| uint simd_group_index, \ | uint simd_group_index, \ | ||||
| uint num_simd_groups) ccl_global const; \ | uint num_simd_groups) ccl_global const; \ | ||||
| }; \ | }; \ | ||||
| kernel void kernel_metal_##name(device const kernel_gpu_##name *params_struct, \ | kernel void cycles_metal_##name(device const kernel_gpu_##name *params_struct, \ | ||||
| constant KernelParamsMetal &ccl_restrict _launch_params_metal, \ | constant KernelParamsMetal &ccl_restrict _launch_params_metal, \ | ||||
| constant MetalAncillaries *_metal_ancillaries, \ | constant MetalAncillaries *_metal_ancillaries, \ | ||||
| threadgroup int *simdgroup_offset[[ threadgroup(0) ]], \ | threadgroup int *simdgroup_offset[[ threadgroup(0) ]], \ | ||||
| const uint metal_global_id [[thread_position_in_grid]], \ | const uint metal_global_id [[thread_position_in_grid]], \ | ||||
| const ushort metal_local_id [[thread_position_in_threadgroup]], \ | const ushort metal_local_id [[thread_position_in_threadgroup]], \ | ||||
| const ushort metal_local_size [[threads_per_threadgroup]], \ | const ushort metal_local_size [[threads_per_threadgroup]], \ | ||||
| uint simdgroup_size [[threads_per_simdgroup]], \ | uint simdgroup_size [[threads_per_simdgroup]], \ | ||||
| uint simd_lane_index [[thread_index_in_simdgroup]], \ | uint simd_lane_index [[thread_index_in_simdgroup]], \ | ||||
| ▲ Show 20 Lines • Show All 184 Lines • Show Last 20 Lines | |||||