awl::main::exit_code const example_main( awl::main::function_context const &_main_function_context ) try { if( _main_function_context.argc() > 2 ) { fcppt::io::cerr() << FCPPT_TEXT("Pass exactly one argument to show a given text") FCPPT_TEXT(" or pass nothing to see the default text.\n"); return awl::main::exit_failure(); } sge::systems::instance< boost::mpl::vector4< sge::systems::with_renderer< sge::systems::renderer_caps::ffp >, sge::systems::with_window, sge::systems::with_input< boost::mpl::vector1< sge::systems::keyboard_collector > >, sge::systems::with_image2d > > const sys( sge::systems::make_list ( sge::systems::window( sge::systems::window_source( sge::systems::original_window( sge::window::title( FCPPT_TEXT("sge animtest") ) ) ) ) ) ( sge::systems::renderer( sge::renderer::pixel_format::object( sge::renderer::pixel_format::color::depth32, sge::renderer::pixel_format::depth_stencil::off, sge::renderer::pixel_format::optional_multi_samples(), sge::renderer::pixel_format::srgb::no ), sge::renderer::display_mode::parameters( sge::renderer::display_mode::vsync::on, sge::renderer::display_mode::optional_object() ), sge::viewport::optional_resize_callback{ sge::viewport::center_on_resize( sge::window::dim{ 1024u, 768u } ) } ) ) ( sge::systems::input( sge::systems::cursor_option_field::null() ) ) ( sge::systems::image2d( sge::media::optional_extension_set( sge::media::extension_set{ sge::media::extension( FCPPT_TEXT("png") ) } ) ) ) ); sge::font::object_unique_ptr const font_object( sge::font::bitmap::create( sys.log_context(), sge::config::media_path() / FCPPT_TEXT("fonts") / FCPPT_TEXT("bitmap") / FCPPT_TEXT("font.json"), sys.image_system() ) ); fcppt::signal::auto_connection const escape_connection( sge::systems::quit_on_escape( sys ) ); sge::font::string const string( _main_function_context.argc() == 2 ? sge::font::from_fcppt_string( fcppt::from_std_string( _main_function_context.argv()[1] ) ) : SGE_FONT_LIT("test abcd e 123456789 10 11") ); sge::font::draw::static_text static_text_left( sys.renderer_device_ffp(), *font_object, string, sge::font::text_parameters( sge::font::align_h::variant( sge::font::align_h::left( sge::font::align_h::max_width( 300 ) ) ) ), sge::font::vector( 100, 100 ), sge::image::color::predef::white(), sge::renderer::texture::emulate_srgb::yes ); sge::font::draw::static_text static_text_center( sys.renderer_device_ffp(), *font_object, string, sge::font::text_parameters( sge::font::align_h::variant( sge::font::align_h::center( sge::font::align_h::max_width( 300 ) ) ) ), sge::font::vector( 400, 100 ), sge::image::color::predef::white(), sge::renderer::texture::emulate_srgb::yes ); sge::font::draw::static_text static_text_right( sys.renderer_device_ffp(), *font_object, string, sge::font::text_parameters( sge::font::align_h::variant( sge::font::align_h::right( sge::font::align_h::max_width( 300 ) ) ) ), sge::font::vector( 700, 100 ), sge::image::color::predef::white(), sge::renderer::texture::emulate_srgb::yes ); while( sys.window_system().poll() ) { sge::renderer::context::scoped_ffp const scoped_block( sys.renderer_device_ffp(), sys.renderer_device_ffp().onscreen_target() ); scoped_block.get().clear( sge::renderer::clear::parameters() .back_buffer( sge::image::color::predef::black() ) ); static_text_left.draw( scoped_block.get() ); static_text_center.draw( scoped_block.get() ); static_text_right.draw( scoped_block.get() ); } return sys.window_system().exit_code(); } catch( fcppt::exception const &_exception ) { fcppt::io::cerr() << _exception.string() << FCPPT_TEXT('\n'); return awl::main::exit_failure(); } catch( std::exception const &_exception ) { std::cerr << _exception.what() << '\n'; return awl::main::exit_failure(); }
int main() try { sge::opencl::system opencl_system; fcppt::io::cout() << FCPPT_TEXT("Querying the number of available platforms...\n"); sge::opencl::platform::object_sequence &platforms( opencl_system.platforms()); if(platforms.empty()) { fcppt::io::cerr() << FCPPT_TEXT("Couldn't find any OpenCL platforms on your system.\n"); return EXIT_FAILURE; } fcppt::io::cout() << FCPPT_TEXT("Number of OpenCL platforms: ") << platforms.size() << FCPPT_TEXT("\n") << FCPPT_TEXT("Platform listing begin:\n") << FCPPT_TEXT("-----------------------\n"); sge::opencl::platform::object_sequence::size_type platform_index = 0; for( sge::opencl::platform::object const ¤t_platform : platforms ) { fcppt::io::cout() << FCPPT_TEXT("\tPlatform ") << platform_index++ << FCPPT_TEXT(":\n") << FCPPT_TEXT("\tName: ") << fcppt::from_std_string( current_platform.name() ) << FCPPT_TEXT("\n") << FCPPT_TEXT("\tVendor: ") << fcppt::from_std_string( current_platform.vendor() ) << FCPPT_TEXT("\n") << FCPPT_TEXT("Profile type: ") << (current_platform.profile() == sge::opencl::platform::profile_type::full ? fcppt::string(FCPPT_TEXT("full")) : fcppt::string(FCPPT_TEXT("embedded"))) << FCPPT_TEXT("\n") << FCPPT_TEXT("\tVersion: ") << current_platform.version().major_part() << FCPPT_TEXT(".") << current_platform.version().minor_part() << FCPPT_TEXT("\n"); if(!current_platform.version().platform_specific().empty()) fcppt::io::cout() << FCPPT_TEXT("\tPlatform specific version info: ") << fcppt::from_std_string(current_platform.version().platform_specific()) << FCPPT_TEXT("\n"); fcppt::io::cout() << FCPPT_TEXT("\tExtension list begin:\n") << FCPPT_TEXT("\t*********************\n") << FCPPT_TEXT("\t\t") << fcppt::from_std_string( boost::algorithm::join( current_platform.extensions(), std::string("\n\t\t"))) << FCPPT_TEXT("\r\t*********************\n") << FCPPT_TEXT("-----------------------\n"); } fcppt::io::cout() << FCPPT_TEXT("Platform listing end\n"); sge::opencl::platform::object_sequence::size_type chosen_platform_index; if(platforms.size() == 1) { chosen_platform_index = 0; } else { fcppt::io::cout() << FCPPT_TEXT("Your choice: "); do chosen_platform_index = query_value_from_user<sge::opencl::platform::object_sequence::size_type>( fcppt::io::cin()); while(chosen_platform_index >= platforms.size()); } fcppt::io::cout() << FCPPT_TEXT("List devices with properties? [y/n] "); fcppt::char_type list_devices; do list_devices = query_value_from_user<fcppt::char_type>( fcppt::io::cin()); while(list_devices != FCPPT_TEXT('y') && list_devices != FCPPT_TEXT('n')); sge::opencl::platform::object &chosen_platform = platforms[chosen_platform_index]; if(list_devices == FCPPT_TEXT('y')) { fcppt::io::cout() << FCPPT_TEXT("Number of devices on this platform: ") << chosen_platform.devices().size() << FCPPT_TEXT('\n') << FCPPT_TEXT("Device listing begin:\n") << FCPPT_TEXT("-----------------------\n"); for( sge::opencl::device::object const ¤t_device : chosen_platform.devices() ) { current_device.output_info( std::cout); fcppt::io::cout() << FCPPT_TEXT("-----------------------\n"); } fcppt::io::cout() << FCPPT_TEXT("-----------------------\n") << FCPPT_TEXT("Device listing end\n"); } fcppt::io::cout() << FCPPT_TEXT("Creating sge::systems object...\n"); sge::window::dim const window_dim{ 1024u, 768u }; sge::systems::instance< brigand::list< sge::systems::with_window, sge::systems::with_renderer< sge::systems::renderer_caps::core > > > const sys( sge::systems::make_list ( // FIXME: Move this higher? sge::systems::config() .log_settings( sge::systems::log_settings{ sge::log::option_container{ sge::log::option{ sge::opencl::log_location(), fcppt::log::level::verbose } } } ) ) ( sge::systems::window( sge::systems::window_source( sge::systems::original_window( sge::window::title( FCPPT_TEXT("Simple OpenCL example") ) ) ) ) .dont_show() ) ( sge::systems::renderer( sge::renderer::pixel_format::object( sge::renderer::pixel_format::color::depth32, sge::renderer::pixel_format::depth_stencil::off, sge::renderer::pixel_format::optional_multi_samples(), sge::renderer::pixel_format::srgb::no ), sge::renderer::display_mode::parameters( sge::renderer::display_mode::vsync::on, sge::renderer::display_mode::optional_object() ), sge::viewport::optional_resize_callback{ sge::viewport::center_on_resize( window_dim ) } ) ) ); fcppt::io::cout() << FCPPT_TEXT("Done. Creating a context with all devices on this platform...\n"); sge::opencl::device::object_ref_sequence const device_refs( fcppt::algorithm::map< sge::opencl::device::object_ref_sequence >( chosen_platform.devices(), []( sge::opencl::device::object &_device ) { return fcppt::make_ref( _device ); } ) ); sge::opencl::context::object main_context( sge::opencl::context::parameters( chosen_platform, device_refs ) .share_with( sys.renderer_device_core()) .error_callback( sge::opencl::context::error_callback{ &opencl_error_callback } ) ); fcppt::io::cout() << FCPPT_TEXT("Context created, listing available planar image formats (read/write)\n"); sge::opencl::memory_object::image::format_sequence const planar_image_formats = main_context.supported_planar_image_formats( CL_MEM_READ_WRITE); for( auto const format : planar_image_formats ) { sge::opencl::memory_object::image::format_output( std::cout, format ); std::cout << '\n'; } fcppt::io::cout() << FCPPT_TEXT("Listing available volume image formats (read/write)...\n"); sge::opencl::memory_object::image::format_sequence const volume_image_formats = main_context.supported_volume_image_formats( CL_MEM_READ_WRITE); for( auto const format : volume_image_formats ) { sge::opencl::memory_object::image::format_output( std::cout, format ); std::cout << '\n'; } fcppt::io::cout() << FCPPT_TEXT("Done, now creating a program..."); sge::opencl::program::object main_program( sys.log_context(), main_context, sge::opencl::program::source_string_sequence{ std::string( "__kernel void hello_kernel(" "float const multiplier," "__global float *input)" "{" "int gid = get_global_id(0);" "int lid = get_local_id(0);" "input[gid] = lid * multiplier;" "}" ) }, sge::opencl::program::optional_build_parameters()); fcppt::io::cout() << FCPPT_TEXT("Program created, building the program...\n"); volatile bool build_finished = false; main_program.build( sge::opencl::program::build_parameters() .notification_callback( sge::opencl::program::notification_callback{ std::bind( &program_build_finished, std::ref( build_finished ) ) } ) ); std::cout << "Waiting for build completion\n"; while(!build_finished) std::cout << "Build not finished yet\n"; fcppt::io::cout() << FCPPT_TEXT("Program built, now creating a kernel...\n"); sge::opencl::kernel::object main_kernel( main_program, sge::opencl::kernel::name( "hello_kernel")); fcppt::io::cout() << FCPPT_TEXT("Kernel created, now creating a vertex buffer...\n"); sge::renderer::vertex::declaration_unique_ptr const vertex_declaration( sys.renderer_device_core().create_vertex_declaration( sge::renderer::vertex::declaration_parameters( sge::renderer::vf::dynamic::make_format<vf::format>()))); sge::renderer::vertex::buffer_unique_ptr const vb( sys.renderer_device_core().create_vertex_buffer( sge::renderer::vertex::buffer_parameters( *vertex_declaration, sge::renderer::vf::dynamic::make_part_index< vf::format, vf::part >(), sge::renderer::vertex::count( 6u), sge::renderer::resource_flags_field{ sge::renderer::resource_flags::readable}))); fcppt::io::cout() << FCPPT_TEXT("Done, now creating OpenCL buffer from it\n"); sge::opencl::memory_object::buffer cl_vb( main_context, *vb, sge::opencl::memory_object::renderer_buffer_lock_mode::write_only); main_kernel.argument( sge::opencl::kernel::argument_index( 1u), cl_vb); main_kernel.argument( sge::opencl::kernel::argument_index( 0u), sge::opencl::kernel::numeric_type( static_cast<cl_float>( 2.0 ) ) ); fcppt::io::cout() << FCPPT_TEXT("Done, now creating a command queue\n"); sge::opencl::command_queue::object main_queue( device_refs[0].get(), main_context, sge::opencl::command_queue::execution_mode::out_of_order, sge::opencl::command_queue::profiling_mode::disabled); fcppt::io::cout() << FCPPT_TEXT("Done, now enqueueing kernel and running it\n"); { sge::opencl::memory_object::scoped_objects scoped_vb( main_queue, sge::opencl::memory_object::base_ref_sequence{ fcppt::reference_to_base< sge::opencl::memory_object::base >( fcppt::make_ref( cl_vb ) ) } ); sge::opencl::command_queue::enqueue_kernel( main_queue, main_kernel, sge::opencl::command_queue::global_dim1( sge::opencl::dim1( vb->linear_size() * 2u ) ), sge::opencl::command_queue::local_dim1( sge::opencl::dim1( 2u ) ), sge::opencl::event::sequence() ); } fcppt::io::cout() << FCPPT_TEXT("Now locking the vb for reading and printing the values\n"); { sge::renderer::vertex::scoped_lock const scoped_vb( *vb, sge::renderer::lock_mode::readwrite); typedef sge::renderer::vf::view<vf::part> vertex_view; vertex_view const vertices( scoped_vb.value()); for( auto const vertex : vertices ) { fcppt::io::cout() << vertex.get<vf::scalar_quantity>() << FCPPT_TEXT('\n'); } } fcppt::io::cout() << FCPPT_TEXT("Done\n"); } catch( fcppt::exception const &_error ) { fcppt::io::cerr() << _error.string() << FCPPT_TEXT('\n'); return EXIT_FAILURE; } catch( std::exception const &_error ) { std::cerr << _error.what() << '\n'; return EXIT_FAILURE; }