RAJA
RAJA provides a collection of platform portability abstractions for C++ HPC applications.
Classes | Namespaces | Typedefs | Functions | Variables
launch.hpp File Reference

RAJA header file containing user interface for RAJA::launch::cuda. More...

#include "RAJA/pattern/launch/launch_core.hpp"
#include "RAJA/pattern/detail/privatizer.hpp"
#include "RAJA/policy/cuda/policy.hpp"
#include "RAJA/policy/cuda/MemUtils_CUDA.hpp"
#include "RAJA/policy/cuda/raja_cudaerrchk.hpp"
#include "RAJA/util/resource.hpp"

Go to the source code of this file.

Classes

class  RAJA::LaunchContextT< cuda::LaunchContextIndicesAndDimsPolicy< IndicesAndDimsT > >
 
struct  RAJA::LaunchExecute< RAJA::policy::cuda::cuda_launch_explicit_t< async, named_usage::unspecified, named_usage::unspecified > >
 
struct  RAJA::LaunchExecute< RAJA::policy::cuda::cuda_launch_explicit_t< async, nthreads, BLOCKS_PER_SM > >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopICountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::DirectUnchecked, sync, IndexMapper0 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::Direct, sync, IndexMapper0 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, sync, IndexMapper0 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::LoopExecute< RAJA::policy::cuda::cuda_flatten_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::TileExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::DirectUnchecked, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::Direct, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1 >, SEGMENT >
 
struct  RAJA::TileTCountExecute< RAJA::policy::cuda::cuda_indexer< RAJA::iteration_mapping::StridedLoop< named_usage::unspecified >, kernel_sync_requirement::none, IndexMapper0, IndexMapper1, IndexMapper2 >, SEGMENT >
 

Namespaces

 RAJA
 

Typedefs

using RAJA::LaunchContextType = typename RAJA::detail::launch_context_type< BODY >::type
 

Functions

template<typename BODY , typename ReduceParams >
__global__ void RAJA::launch_new_reduce_global_fcn (const RAJA_CUDA_GRID_CONSTANT BODY body_in, ReduceParams reduce_params)
 
template<typename BODY , int num_threads, size_t BLOCKS_PER_SM, typename ReduceParams >
 RAJA::__launch_bounds__ (num_threads, BLOCKS_PER_SM) __global__ void launch_new_reduce_global_fcn_fixed(const RAJA_CUDA_GRID_CONSTANT BODY body_in
 

Variables

ReduceParams RAJA::reduce_params
 
auto RAJA::privatizer = thread_privatize(body_in)
 
auto & RAJA::body = privatizer.get_priv()
 
__shared__ char RAJA::raja_shmem_ptr []
 
LaunchContextType RAJA::ctx
 
ctx RAJA::shared_mem_ptr = raja_shmem_ptr
 

Detailed Description

RAJA header file containing user interface for RAJA::launch::cuda.

Generated by doxygen 1.9.1