Blender  V2.93
Macros | Functions | Variables
kernel_split_function.h File Reference

Go to the source code of this file.

Macros

#define KERNEL_NAME_JOIN(a, b)   a##_##b
 
#define KERNEL_NAME_EVAL(a, b)   KERNEL_NAME_JOIN(a, b)
 

Functions

__kernel void KERNEL_NAME_EVAL (kernel_ocl_path_trace, KERNEL_NAME)(ccl_global char *kg_global
 
 if (ccl_local_id(0)+ccl_local_id(1)==0)
 
 kernel_set_buffer_pointers (kg, KERNEL_BUFFER_ARGS)
 

Variables

__kernel void ccl_constant KernelDatadata
 
__kernel void ccl_constant KernelData ccl_global void * split_data_buffer
 
__kernel void ccl_constant KernelData ccl_global void ccl_global char * ray_state
 
__kernel void ccl_constant KernelData ccl_global void ccl_global char KERNEL_BUFFER_PARAMS
 
__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int * queue_index
 
__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int ccl_global char * use_queues_flag
 
__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int ccl_global char ccl_global unsigned int * work_pools
 
__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int ccl_global char ccl_global unsigned int ccl_global floatbuffer
 
 kg
 

Macro Definition Documentation

◆ KERNEL_NAME_EVAL

#define KERNEL_NAME_EVAL (   a,
 
)    KERNEL_NAME_JOIN(a, b)

Definition at line 18 of file kernel_split_function.h.

◆ KERNEL_NAME_JOIN

#define KERNEL_NAME_JOIN (   a,
 
)    a##_##b

Definition at line 17 of file kernel_split_function.h.

Function Documentation

◆ if()

if ( ccl_local_id(0)+ccl_local_id(1)  = = 0)

◆ KERNEL_NAME_EVAL()

__kernel void KERNEL_NAME_EVAL ( kernel_ocl_path_trace  ,
KERNEL_NAME   
)

◆ kernel_set_buffer_pointers()

kernel_set_buffer_pointers ( kg  ,
KERNEL_BUFFER_ARGS   
)

Referenced by kernel_data_init().

Variable Documentation

◆ buffer

__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int ccl_global char ccl_global unsigned int ccl_global float* buffer
Initial value:
{
KernelGlobals *kg = (KernelGlobals *)kg_global

Definition at line 32 of file kernel_split_function.h.

Referenced by _bli_buffer_append_array(), _bli_buffer_free(), iTaSC::CacheChannel::_findBlock(), CPUDevice::adaptive_sampling_filter(), CPUDevice::adaptive_sampling_post(), blender::fn::mf_network_optimization::add_constant_folded_sockets(), blender::fn::GValueMap< Key >::add_new_by_copy(), blender::fn::GValueMap< Key >::add_new_by_move(), blender::compositor::NodeGraph::add_proxies_group_outputs(), iTaSC::Cache::addCacheItem(), allocate_arrays(), blender::compositor::ExecutionGroup::allocateOutputBuffer(), iTaSC::CacheChannel::allocBuffer(), MD5Hash::append_file(), avi_converter_from_avi_rgb(), avi_converter_from_mjpeg(), avi_converter_from_rgb32(), avi_converter_to_avi_rgb(), avi_converter_to_mjpeg(), avi_converter_to_rgb32(), avi_format_convert(), AVI_read_frame(), AVI_write_frame(), bake(), BGL_BufferOrOffsetConverter(), BGL_MakeBuffer(), BGL_MakeBuffer_FromData(), BKE_gpencil_modifier_set_error(), BKE_maskrasterize_buffer(), BKE_modifier_set_error(), BKE_subdiv_eval_limit_patch_resolution_point(), BKE_text_load_ex(), BKE_text_reload(), BLI_bicubic_interpolation_char(), BLI_bicubic_interpolation_fl(), BLI_bilinear_interpolation_char(), BLI_bilinear_interpolation_fl(), BLI_bilinear_interpolation_wrap_char(), BLI_bilinear_interpolation_wrap_fl(), BLI_buffer_reinit(), BLI_buffer_resize(), BLI_fstat(), BLI_getenv(), BLI_hash_md5_buffer(), BLI_hash_md5_stream(), BLI_hostname_get(), BLI_stat(), BLI_system_backtrace(), BLI_vsnprintf(), BLI_vsnprintf_rlen(), bli_windows_get_module_name(), bli_windows_get_module_version(), bone_mouse_select_menu(), bpy_prop_string_get_fn(), bpy_slot_to_py(), BPyGPU_Buffer_CreatePyObject(), bpygpu_Buffer_size(), btDefaultSerializer::btDefaultSerializer(), buffer_alloc(), buffer_apply_offset(), Buffer_new(), buffer_realloc(), buffer_write_float_value(), buffer_write_short_value(), Freestyle::BufferedStyleModule::BufferedStyleModule(), blender::compositor::CalculateMeanOperation::calculateMean(), check_pixel_assigned(), iTaSC::CacheChannel::clear(), iTaSC::Cache::clearCacheFrom(), blender::deg::color_for_pointer(), console_cursor_set_exit(), blender::LinearAllocator< Allocator >::construct(), blender::nodes::MFNetworkBuilderBase::construct_fn(), convert_to_byte(), convert_to_half_float(), blender::LinearAllocator< Allocator >::copy_string(), blender::io::alembic::create_abc_metadata(), data_source_send(), CPUDevice::denoise_openimagedenoise_buffer(), display_buffer_apply_threaded(), do_armature_box_select(), do_meta_box_select(), DRW_sparse_uniform_buffer_bind(), DRW_sparse_uniform_buffer_clear(), DRW_sparse_uniform_buffer_ensure_item(), DRW_sparse_uniform_buffer_flush(), DRW_sparse_uniform_buffer_free(), drw_sparse_uniform_buffer_get_ubo(), drw_sparse_uniform_buffer_init(), DRW_sparse_uniform_buffer_is_empty(), DRW_sparse_uniform_buffer_unbind(), DRW_uniform_attrs_pool_clear_all(), drw_uniform_attrs_pool_ensure(), DRW_uniform_attrs_pool_find_ubo(), DRW_uniform_attrs_pool_flush_all(), drw_uniform_attrs_pool_free_cb(), drw_uniform_attrs_pool_update(), ED_armature_pick_bone_from_selectbuffer(), ed_armature_pick_bone_from_selectbuffer_impl(), ed_armature_pick_bone_impl(), ED_armature_pick_ebone_from_selectbuffer(), ED_armature_pick_pchan_from_selectbuffer(), ED_armature_pose_select_pick_with_buffer(), ED_mask_draw_region(), ED_mball_select_pick(), ed_object_select_pick(), ED_view3d_give_base_under_cursor(), edit_uv_mask_texture(), blender::compositor::BufferLineAccumulator< fxu, fxv, fyu, fyv >::eval(), blender::compositor::AntiAliasOperation::executePixel(), blender::compositor::BokehBlurOperation::executePixel(), blender::compositor::DilateErodeThresholdOperation::executePixel(), blender::compositor::DilateDistanceOperation::executePixel(), blender::compositor::ErodeDistanceOperation::executePixel(), blender::compositor::DoubleEdgeMaskOperation::executePixel(), blender::compositor::GaussianAlphaXBlurOperation::executePixel(), blender::compositor::GaussianAlphaYBlurOperation::executePixel(), blender::compositor::GaussianBokehBlurOperation::executePixel(), blender::compositor::GaussianBlurReferenceOperation::executePixel(), blender::compositor::GaussianXBlurOperation::executePixel(), blender::compositor::GaussianYBlurOperation::executePixel(), blender::compositor::IDMaskOperation::executePixel(), blender::compositor::KeyingBlurOperation::executePixel(), blender::compositor::KeyingClipOperation::executePixel(), blender::compositor::ScreenLensDistortionOperation::executePixel(), blender::compositor::VectorBlurOperation::executePixel(), blender::compositor::CompositorOperation::executeRegion(), blender::compositor::ViewerOperation::executeRegion(), blender::compositor::WriteBufferOperation::executeRegion(), blender::fn::GVectorArray::extend(), fcurve_is_changed(), fd_read_data_from_file(), fd_read_from_memfile(), fd_read_from_memory(), fd_read_from_mmap(), fd_read_gzip_from_file(), fd_read_gzip_from_memory(), film_get_pass_result(), filter_construct_transform(), filter_finalize(), filter_get_color(), filter_get_feature_scales(), filter_get_features(), filter_nlm_construct_gramian(), filter_write_feature(), blender::compositor::ExecutionGroup::finalizeChunkExecution(), iTaSC::CacheChannel::findItemEarlier(), iTaSC::CacheChannel::findItemOrLater(), libmv::FloatImageToUCharArray(), free_arrays(), blender::bke::ConvertedReadAttribute::get_internal(), get_keyframe_values(), get_nearest_editbonepoint(), blender::fn::MFNetworkEvaluationStorage::get_single_output__full(), blender::fn::MFNetworkEvaluationStorage::get_single_output__single(), GHOST_SystemWin32::getClipboard(), GHOST_SystemX11::getClipboard_xcout(), iTaSC::Cache::getPreviousCacheItem(), getProcessName(), GHOST_putClipboard(), gizmo_find_intersected_3d_intern(), blender::fn::GMutableSpan::GMutableSpan(), GPU_backbuffer_bind(), GPU_select_begin(), GPU_select_buffer_near(), GPU_select_buffer_remove_by_id(), gpu_select_pick_begin(), gpu_select_query_begin(), blender::fn::GSpan::GSpan(), ibJpegImageFromCinfo(), idp_from_PySequence(), idp_from_PySequence_Buffer(), if(), blender::compositor::FastGaussianBlurOperation::IIR_gauss(), IMB_colormanagement_buffer_make_display_space(), IMB_colormanagement_colorspace_to_scene_linear(), IMB_colormanagement_processor_apply(), IMB_colormanagement_processor_apply_byte(), IMB_colormanagement_transform(), IMB_colormanagement_transform_byte(), IMB_colormanagement_transform_byte_threaded(), IMB_colormanagement_transform_threaded(), IMB_display_buffer_transform_apply(), IMB_index_builder_proc_frame(), imb_load_jpeg(), IMB_rect_from_float(), indirect_background(), init_test_curve(), btAlignedObjectArray< T >::initializeFromBuffer(), blender::compositor::BokehBlurOperation::initializeTileData(), blender::compositor::CalculateStandardDeviationOperation::initializeTileData(), blender::compositor::DilateErodeThresholdOperation::initializeTileData(), blender::compositor::DilateDistanceOperation::initializeTileData(), blender::compositor::DilateStepOperation::initializeTileData(), blender::compositor::ErodeStepOperation::initializeTileData(), blender::compositor::GaussianAlphaXBlurOperation::initializeTileData(), blender::compositor::GaussianAlphaYBlurOperation::initializeTileData(), blender::compositor::GaussianBokehBlurOperation::initializeTileData(), blender::compositor::GaussianBlurReferenceOperation::initializeTileData(), blender::compositor::GaussianXBlurOperation::initializeTileData(), blender::compositor::GaussianYBlurOperation::initializeTileData(), blender::compositor::IDMaskOperation::initializeTileData(), blender::compositor::KeyingBlurOperation::initializeTileData(), blender::compositor::KeyingClipOperation::initializeTileData(), blender::compositor::NormalizeOperation::initializeTileData(), blender::compositor::ProjectorLensDistortionOperation::initializeTileData(), blender::compositor::ScreenLensDistortionOperation::initializeTileData(), blender::compositor::SunBeamsOperation::initializeTileData(), blender::compositor::TonemapOperation::initializeTileData(), intersectRectQuad2(), KDL::IOTracePopStr(), jpegmemdestmgr_build(), jpegmemsrcmgr_build(), kernel_adaptive_adjust_samples(), kernel_adaptive_post_adjust(), kernel_adaptive_stopping(), kernel_buffer_update(), kernel_data_init(), kernel_do_adaptive_filter_x(), kernel_do_adaptive_filter_y(), kernel_do_adaptive_stopping(), kernel_film_convert_to_byte(), kernel_film_convert_to_half_float(), kernel_filter_construct_gramian(), kernel_filter_finalize(), kernel_filter_nlm_construct_gramian(), kernel_filter_write_feature(), kernel_holdout_emission_blurring_pathtermination_ao(), kernel_indirect_background(), kernel_path_background(), kernel_path_integrate(), kernel_path_shader_apply(), kernel_path_trace(), kernel_shader_eval(), kernel_sort_id_slots(), kernel_write_data_passes(), kernel_write_id_slots(), kernel_write_id_slots_gpu(), kernel_write_light_passes(), kernel_write_pass_float(), kernel_write_pass_float3(), kernel_write_pass_float4(), kernel_write_result(), libmv_byteBufferToFloatImage(), libmv_floatBufferToFloatImage(), libmv_floatImageToByteBuffer(), libmv_floatImageToFloatBuffer(), load_tex(), load_tex_cursor(), load_tex_cursor_task_cb(), load_tex_task_cb_ex(), logimage_fread(), logimage_fwrite(), logImageIsCineon(), logImageIsDpx(), logImageOpenFromMemory(), mask_rasterize(), maskrasterize_buffer_cb(), md5_process_block(), memory_source(), mixed_bones_object_selectbuffer(), mixed_bones_object_selectbuffer_extended(), mouse_select_eval_buffer(), nextLine(), object_mouse_select_menu(), OutputAttributePtr::OutputAttributePtr(), path_trace(), prepare(), blender::fn::mf_network_optimization::prepare_params_for_constant_folding(), blender::LinearAllocator< Allocator >::provide_buffer(), GHOST_SystemSDL::putClipboard(), GHOST_SystemWin32::putClipboard(), GHOST_SystemX11::putClipboard(), GHOST_SystemWayland::putClipboard(), pygpu_buffer__tp_new(), pygpu_buffer_make_from_data(), pygpu_shader_uniform_vector_impl(), blender::compositor::MemoryBuffer::read(), blender::compositor::read_ewa_pixel_sampled(), read_pipe(), blender::compositor::MemoryBuffer::readNoCheck(), rna_alloc_from_buffer(), rna_alloc_function_name(), rna_construct_function_name(), rna_construct_wrapper_function_name(), selectbuffer_has_bones(), selectbuffer_ret_hits_5(), selectbuffer_ret_hits_9(), set_cursor_buffer(), blender::opensubdiv::CpuEvalOutputAPI::setCoarsePositionsFromBuffer(), GHOST_SystemWayland::setCursorShape(), GHOST_SystemWayland::setCustomCursorShape(), blender::opensubdiv::CpuEvalOutputAPI::setFaceVaryingDataFromBuffer(), setting_get_rna_values(), blender::opensubdiv::CpuEvalOutputAPI::setVaryingDataFromBuffer(), shader_eval_surface(), blender::nodes::socket_expand_in_mf_network(), btDefaultSerializer::startSerialization(), svm_eval_nodes(), svm_node_aov_check(), svm_node_aov_color(), svm_node_aov_value(), blender::tests::TEST(), blender::fn::tests::TEST(), text_cursor_set_exit(), text_from_buf(), txt_insert_buf(), view3d_opengl_select(), view3d_opengl_select_with_id_filter(), view3d_select_exec(), visualkey_get_values(), blender::compositor::write_buffer_rect(), write_external_bake_pixels(), write_internal_bake_pixels(), write_jpeg(), blender::io::alembic::write_mcol(), btDefaultSerializer::writeHeader(), and OCIO_GPUCurveMappping::~OCIO_GPUCurveMappping().

◆ data

__kernel void ccl_constant KernelData* data

Definition at line 22 of file kernel_split_function.h.

Referenced by if().

◆ KERNEL_BUFFER_PARAMS

__kernel void ccl_constant KernelData ccl_global void ccl_global char KERNEL_BUFFER_PARAMS

Definition at line 27 of file kernel_split_function.h.

◆ kg

kg

Definition at line 58 of file kernel_split_function.h.

Referenced by _shader_bsdf_multi_eval(), CPUDevice::adaptive_sampling_filter(), CPUDevice::adaptive_sampling_post(), attribute_primitive_type(), bake(), bsdf_eval(), bsdf_microfacet_beckmann_sample(), bsdf_microfacet_ggx_sample(), bsdf_principled_hair_eval(), bsdf_principled_hair_sample(), bsdf_sample(), BVH(), BVH_FUNCTION_NAME(), bvh_instance_pop(), bvh_instance_pop_factor(), bvh_instance_push(), bvh_node_intersect(), bvh_unaligned_node_intersect(), bvh_unaligned_node_intersect_child(), camera_sample(), camera_world_to_ndc(), combine_with_energy(), convert_to_byte(), convert_to_half_float(), direct_emission(), direct_emissive_eval(), CPUSplitKernelFunction::enqueue(), CPUSplitKernel::enqueue_split_kernel_data_init(), find_attribute(), find_attribute_motion(), OSLRenderServices::get_attribute(), OSLRenderServices::get_background_attribute(), OSLRenderServices::get_inverse_matrix(), OSLRenderServices::get_matrix(), get_mesh_attribute(), OSLRenderServices::get_object_standard_attribute(), get_primitive_attribute(), OSLRenderServices::getmessage(), hair_attenuation(), if(), indirect_background(), indirect_lamp_emission(), indirect_primitive_emission(), kernel_adaptive_adjust_samples(), kernel_adaptive_filter_x(), kernel_adaptive_filter_y(), kernel_adaptive_stopping(), kernel_background_evaluate(), kernel_buffer_update(), kernel_const_copy(), kernel_data_init(), kernel_direct_lighting(), kernel_displace_evaluate(), kernel_do_volume(), kernel_film_convert_to_byte(), kernel_film_convert_to_half_float(), kernel_holdout_emission_blurring_pathtermination_ao(), kernel_ies_interp(), kernel_indirect_background(), kernel_indirect_subsurface(), kernel_lamp_emission(), kernel_next_iteration_setup(), kernel_path_ao(), kernel_path_background(), kernel_path_init(), kernel_path_integrate(), kernel_path_lamp_emission(), kernel_path_scene_intersect(), kernel_path_shader_apply(), kernel_path_surface_bounce(), kernel_path_surface_connect_light(), kernel_path_trace(), kernel_path_trace_setup(), kernel_scene_intersect(), kernel_shader_eval(), kernel_shader_setup(), kernel_shadow_blocked_ao(), kernel_shadow_blocked_dl(), kernel_subsurface_scatter(), kernel_tex_image_interp(), kernel_tex_image_interp_3d(), kernel_tex_info(), kernel_write_data_passes(), kernel_write_result(), lamp_light_eval(), lamp_light_sample(), light_sample(), lookup_table_read_2D(), DeviceSplitKernel::max_elements_for_max_buffer_size(), microfacet_beckmann_sample_slopes(), microfacet_sample_stretched(), motion_triangle_intersect(), motion_triangle_refine(), motion_triangle_shader_setup(), motion_triangle_smooth_normal(), motion_triangle_vertices(), object_dir_transform(), object_inverse_dir_transform(), object_inverse_normal_transform(), object_inverse_position_transform(), object_location(), object_normal_transform(), object_position_transform(), patch_eval_control_verts(), patch_eval_float(), patch_eval_float2(), patch_eval_float3(), patch_eval_float4(), patch_eval_uchar4(), patch_map_find_patch(), path_branched_rng_1D(), path_branched_rng_2D(), path_branched_rng_light_termination(), path_radiance_accum_background(), path_radiance_accum_emission(), path_radiance_accum_light(), path_radiance_clamp_and_sum(), path_rng_1D(), path_rng_2D(), path_rng_init(), path_state_init(), path_state_rng_1D(), path_state_rng_1D_hash(), path_state_rng_2D(), path_state_rng_light_termination(), path_trace(), primitive_motion_vector(), primitive_ptex(), primitive_surface_attribute_float(), primitive_surface_attribute_float2(), primitive_surface_attribute_float3(), primitive_surface_attribute_float4(), primitive_tangent(), primitive_uv(), CPUDevice::render(), rgb_ramp_lookup(), scene_intersect(), shader(), shader_bsdf_alpha(), shader_bsdf_blur(), shader_bsdf_eval(), shader_bsdf_sample(), shader_bsdf_sample_closure(), shader_eval_displacement(), shader_eval_surface(), shader_setup_from_background(), shader_setup_from_displace(), shader_setup_from_ray(), shader_setup_from_sample(), shaderdata_to_shaderglobals(), shadow_blocked(), shadow_blocked_opaque(), shadow_handle_transparent_isect(), CBSDFClosure::skip(), sky_radiance_hosek(), sky_radiance_nishita(), sky_radiance_preetham(), split_data_buffer_size(), split_data_init(), CPUSplitKernel::state_buffer_size(), subd_triangle_attribute_float(), subd_triangle_attribute_float2(), subd_triangle_attribute_float3(), subd_triangle_attribute_float4(), subsurface_color_bump_blur(), subsurface_random_walk(), subsurface_scatter_disk(), subsurface_scatter_multi_intersect(), subsurface_scatter_multi_setup(), svm_eval_nodes(), svm_image_texture(), svm_image_texture_read_2d(), svm_image_texture_read_3d(), svm_node_attr(), svm_node_attr_bump_dx(), svm_node_attr_bump_dy(), svm_node_attr_init(), svm_node_clamp(), svm_node_closure_bsdf(), svm_node_combine_hsv(), svm_node_convert(), svm_node_curves(), svm_node_displacement(), svm_node_enter_bump_eval(), svm_node_geometry(), svm_node_geometry_bump_dx(), svm_node_geometry_bump_dy(), svm_node_ies(), svm_node_map_range(), svm_node_min_max(), svm_node_mix(), svm_node_normal(), svm_node_normal_map(), svm_node_object_info(), svm_node_particle_info(), svm_node_principled_volume(), svm_node_rgb_ramp(), svm_node_separate_hsv(), svm_node_set_bump(), svm_node_tangent(), svm_node_tex_brick(), svm_node_tex_coord(), svm_node_tex_coord_bump_dx(), svm_node_tex_coord_bump_dy(), svm_node_tex_environment(), svm_node_tex_image(), svm_node_tex_image_box(), svm_node_tex_magic(), svm_node_tex_musgrave(), svm_node_tex_noise(), svm_node_tex_sky(), svm_node_tex_voronoi(), svm_node_tex_voxel(), svm_node_tex_wave(), svm_node_texture_mapping(), svm_node_value_v(), svm_node_vector_displacement(), svm_node_vector_math(), svm_node_vector_transform(), svm_node_vertex_color(), svm_node_vertex_color_bump_dx(), svm_node_vertex_color_bump_dy(), svm_node_wavelength(), svm_node_wireframe(), CPUDevice::thread_kernel_globals_free(), CPUDevice::thread_kernel_globals_init(), CPUDevice::thread_render(), CPUDevice::thread_shader(), OSLRenderServices::trace(), triangle_intersect(), triangle_light_pdf(), triangle_light_sample(), triangle_refine(), triangle_refine_local(), triangle_world_space_vertices(), and wireframe().

◆ queue_index

__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int* queue_index

◆ ray_state

__kernel void ccl_constant KernelData ccl_global void ccl_global char* ray_state

◆ split_data_buffer

__kernel void ccl_constant KernelData ccl_global void* split_data_buffer

Definition at line 24 of file kernel_split_function.h.

Referenced by if(), and kernel_data_init().

◆ use_queues_flag

__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int ccl_global char* use_queues_flag

Definition at line 30 of file kernel_split_function.h.

Referenced by if(), and kernel_data_init().

◆ work_pools

__kernel void ccl_constant KernelData ccl_global void ccl_global char ccl_global int ccl_global char ccl_global unsigned int* work_pools