algorithms.h File Reference

#include "common.h"
#include <numeric>
#include <algorithm>
#include <thrust/generate.h>
#include <thrust/sort.h>
#include <thrust/copy.h>
#include <thrust/reduce.h>

Include dependency graph for algorithms.h:

This graph shows which files directly or indirectly include this file:

Go to the source code of this file.

Namespaces
	bc
	The Evaluator determines if an expression needs to be greedily optimized.
	bc::algorithms

Macros
#define	BC_ALGORITHM_DEF(function)
#define	BC_REDUCE_ALGORITHM_DEF(function)
#define	BC_REDUCE_ALGORITHM_DEF_FIX_THRUST(function)
	– thrust fails to compile certain functions. More...

Functions
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto for_each(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::for_each(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::for_each (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto count(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::count(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::count (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto count_if(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::count_if(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::count_if (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto find(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::find(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::find (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto find_if(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::find_if(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::find_if (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto find_if_not(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::find_if_not(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::find_if_not (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto copy(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::copy(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::copy (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto copy_if(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::copy_if(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::copy_if (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto copy_n(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::copy_n(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::copy_n (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto fill(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::fill(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::fill (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto fill_n(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::fill_n(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::fill_n (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto transform(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::transform(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::transform (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto generate(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::generate(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::generate (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto generate_n(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::generate_n(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::generate_n (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto replace(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::replace(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::replace (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto replace_if(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::replace_if(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::replace_if (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto replace_copy(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::replace_copy(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::replace_copy (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto replace_copy_if(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::replace_copy_if(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::replace_copy_if (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto swap(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::swap(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::swap (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto swap_ranges(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::swap_ranges(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::swap_ranges (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto reverse(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::reverse(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::reverse (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto reverse_copy(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::reverse_copy(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::reverse_copy (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto is_sorted(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::is_sorted(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::is_sorted (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto is_sorted_until(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::is_sorted_until(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::is_sorted_until (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto sort(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::sort(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::sort (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto stable_sort(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::stable_sort(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::stable_sort (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto max(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { static_assert(std::is_same< std::random_access_iterator_tag, typename Begin::iterator_category >::value, "Assert random_access_iterator_tag");return thrust::max(thrust::cuda::par.on(stream), &*begin, &*end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::max (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto max_element(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { static_assert(std::is_same< std::random_access_iterator_tag, typename Begin::iterator_category >::value, "Assert random_access_iterator_tag");return thrust::max_element(thrust::cuda::par.on(stream), &*begin, &*end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::max_element (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto min(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { static_assert(std::is_same< std::random_access_iterator_tag, typename Begin::iterator_category >::value, "Assert random_access_iterator_tag");return thrust::min(thrust::cuda::par.on(stream), &*begin, &*end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::min (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto min_element(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { static_assert(std::is_same< std::random_access_iterator_tag, typename Begin::iterator_category >::value, "Assert random_access_iterator_tag");return thrust::min_element(thrust::cuda::par.on(stream), &*begin, &*end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::min_element (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)
	bc::algorithms::BC_IF_CUDA (template< class Begin, class End, class... Args > static auto minmax_element(bc::streams::Stream< bc::device_tag > stream, Begin begin, End end, Args... args) { return thrust::minmax_element(thrust::cuda::par.on(stream), begin, end, args...);}) template< class Begin
class::::::Args static auto	bc::algorithms::minmax_element (bc::streams::Stream< bc::host_tag > stream, Begin begin, End end, Args... args)

Macro Definition Documentation

BC_ALGORITHM_DEF

#define BC_ALGORITHM_DEF

(

function

)

Value:

\
BC_IF_CUDA(                                                               \
template<class Begin, class End, class... Args>                           \
static auto function(                                                     \
        bc::streams::Stream<bc::device_tag> stream,                       \
        Begin begin,                                                      \
        End end,                                                          \
        Args... args)                                                     \
{                                                                         \
    return thrust::function(                                              \
            thrust::cuda::par.on(stream), begin, end, args...);           \
})                                                                        \
                                                                          \
template<class Begin, class End, class... Args>                           \
static auto function (                                                    \
        bc::streams::Stream<bc::host_tag> stream,                         \
        Begin begin,                                                      \
        End end,                                                          \
        Args... args)                                                     \
{                                                                         \
    return stream.enqueue([&](){ std::function(begin, end, args...); });  \
}

BC_REDUCE_ALGORITHM_DEF

#define BC_REDUCE_ALGORITHM_DEF

(

function

)

Value:

BC_IF_CUDA(                                                               \
template<class Begin, class End, class... Args>                           \
static auto function(                                                     \
        bc::streams::Stream<bc::device_tag> stream,                       \
        Begin begin,                                                      \
        End end,                                                          \
        Args... args)                                                     \
{                                                                         \
    return thrust::function(                                              \
            thrust::cuda::par.on(stream), begin, end, args...);           \
})                                                                        \
                                                                          \
template<class Begin, class End, class... Args>                           \
static auto function (                                                    \
        bc::streams::Stream<bc::host_tag> stream,                         \
        Begin begin,                                                      \
        End end,                                                          \
        Args... args)                                                     \
    {                                                                     \
        using value_type = std::decay_t<                                  \
                decltype(std::function(begin, end, args...))>;            \
                                                                          \
        value_type value;                                                 \
        stream.enqueue([&]() {                                            \
                value = std::function(begin, end, args...);               \
        });                                                               \
                                                                          \
        stream.sync();                                                    \
        return value;                                                     \
    }                                                                     \

BC_REDUCE_ALGORITHM_DEF_FIX_THRUST

#define BC_REDUCE_ALGORITHM_DEF_FIX_THRUST

(

function

)

Value:

BC_IF_CUDA(                                                               \
template<class Begin, class End, class... Args>                           \
static auto function(                                                     \
        bc::streams::Stream<bc::device_tag> stream,                       \
        Begin begin,                                                      \
        End end,                                                          \
        Args... args)                                                     \
{                                                                         \
    static_assert(std::is_same<                                           \
            std::random_access_iterator_tag,                              \
            typename Begin::iterator_category>::value,                    \
            "Assert random_access_iterator_tag");                         \
                                                                          \
    return thrust::function(                                              \
            thrust::cuda::par.on(stream), &*begin, &*end, args...);       \
})                                                                        \
                                                                          \
template<class Begin, class End, class... Args>                           \
static auto function (                                                    \
        bc::streams::Stream<bc::host_tag> stream,                         \
        Begin begin,                                                      \
        End end,                                                          \
        Args... args)                                                     \
    {                                                                     \
        bc::streams::host_sync();                                         \
        return &*begin + std::function(begin, end, args...);              \
    }                                                                     \

– thrust fails to compile certain functions.

/usr/local/cuda/bin/.. /targets/x86_64-linux/include/thrust/iterator/detail/zip_iterator_base.h(96): error: qualifiers dropped in binding reference of type "bc::device_tag::default_floating_point_type &"

Likewise functions that returns iterators in thrust may return integers in std::library (namely max_element/min_element), this will always return an iterator therefor unifying the two different interfaces