mirror of https://github.com/GOSTSec/ccminer
You can not select more than 25 topics
Topics must start with a letter or number, can include dashes ('-') and can be up to 35 characters long.
394 lines
8.8 KiB
394 lines
8.8 KiB
/* |
|
* Copyright 2008-2012 NVIDIA Corporation |
|
* |
|
* Licensed under the Apache License, Version 2.0 (the "License"); |
|
* you may not use this file except in compliance with the License. |
|
* You may obtain a copy of the License at |
|
* |
|
* http://www.apache.org/licenses/LICENSE-2.0 |
|
* |
|
* Unless required by applicable law or agreed to in writing, software |
|
* distributed under the License is distributed on an "AS IS" BASIS, |
|
* WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied. |
|
* See the License for the specific language governing permissions and |
|
* limitations under the License. |
|
*/ |
|
|
|
#pragma once |
|
|
|
#include <thrust/detail/config.h> |
|
#include <thrust/detail/functional/actor.h> |
|
#include <thrust/detail/functional/composite.h> |
|
#include <thrust/detail/functional/operators/operator_adaptors.h> |
|
#include <thrust/functional.h> |
|
|
|
namespace thrust |
|
{ |
|
namespace detail |
|
{ |
|
namespace functional |
|
{ |
|
|
|
template<typename Eval> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
unary_operator<thrust::negate>, |
|
actor<Eval> |
|
> |
|
> |
|
__host__ __device__ |
|
operator-(const actor<Eval> &_1) |
|
{ |
|
return compose(unary_operator<thrust::negate>(), _1); |
|
} // end operator-() |
|
|
|
// there's no standard unary_plus functional, so roll an ad hoc one here |
|
template<typename T> |
|
struct unary_plus |
|
: public thrust::unary_function<T,T> |
|
{ |
|
__host__ __device__ T operator()(const T &x) const {return +x;} |
|
}; // end unary_plus |
|
|
|
template<typename Eval> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
unary_operator<unary_plus>, |
|
actor<Eval> |
|
> |
|
> |
|
operator+(const actor<Eval> &_1) |
|
{ |
|
return compose(unary_operator<unary_plus>(), _1); |
|
} // end operator+() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::plus>, |
|
actor<T1>, |
|
typename as_actor<T2>::type |
|
> |
|
> |
|
operator+(const actor<T1> &_1, const T2 &_2) |
|
{ |
|
return compose(binary_operator<thrust::plus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator+() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::plus>, |
|
typename as_actor<T1>::type, |
|
actor<T2> |
|
> |
|
> |
|
operator+(const T1 &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::plus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator+() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::plus>, |
|
actor<T1>, |
|
actor<T2> |
|
> |
|
> |
|
operator+(const actor<T1> &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::plus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator+() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::minus>, |
|
typename as_actor<T1>::type, |
|
actor<T2> |
|
> |
|
> |
|
operator-(const T1 &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::minus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator-() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::minus>, |
|
actor<T1>, |
|
typename as_actor<T2>::type |
|
> |
|
> |
|
operator-(const actor<T1> &_1, const T2 &_2) |
|
{ |
|
return compose(binary_operator<thrust::minus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator-() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::minus>, |
|
actor<T1>, |
|
actor<T2> |
|
> |
|
> |
|
operator-(const actor<T1> &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::minus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator-() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::multiplies>, |
|
typename as_actor<T1>::type, |
|
actor<T2> |
|
> |
|
> |
|
operator*(const T1 &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::multiplies>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator*() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::multiplies>, |
|
actor<T1>, |
|
typename as_actor<T2>::type |
|
> |
|
> |
|
operator*(const actor<T1> &_1, const T2 &_2) |
|
{ |
|
return compose(binary_operator<thrust::multiplies>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator*() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::multiplies>, |
|
actor<T1>, |
|
actor<T2> |
|
> |
|
> |
|
operator*(const actor<T1> &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::multiplies>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator*() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::divides>, |
|
actor<T1>, |
|
typename as_actor<T2>::type |
|
> |
|
> |
|
operator/(const actor<T1> &_1, const T2 &_2) |
|
{ |
|
return compose(binary_operator<thrust::divides>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator/() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::divides>, |
|
typename as_actor<T1>::type, |
|
actor<T2> |
|
> |
|
> |
|
operator/(const T1 &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::divides>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator/() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::divides>, |
|
actor<T1>, |
|
actor<T2> |
|
> |
|
> |
|
operator/(const actor<T1> &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::divides>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator/() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::modulus>, |
|
actor<T1>, |
|
typename as_actor<T2>::type |
|
> |
|
> |
|
operator%(const actor<T1> &_1, const T2 &_2) |
|
{ |
|
return compose(binary_operator<thrust::modulus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator%() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::modulus>, |
|
typename as_actor<T1>::type, |
|
actor<T2> |
|
> |
|
> |
|
operator%(const T1 &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::modulus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator%() |
|
|
|
template<typename T1, typename T2> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
binary_operator<thrust::modulus>, |
|
actor<T1>, |
|
actor<T2> |
|
> |
|
> |
|
operator%(const actor<T1> &_1, const actor<T2> &_2) |
|
{ |
|
return compose(binary_operator<thrust::modulus>(), |
|
make_actor(_1), |
|
make_actor(_2)); |
|
} // end operator%() |
|
|
|
// there's no standard prefix_increment functional, so roll an ad hoc one here |
|
template<typename T> |
|
struct prefix_increment |
|
: public thrust::unary_function<T&,T&> |
|
{ |
|
__host__ __device__ T& operator()(T &x) const { return ++x; } |
|
}; // end prefix_increment |
|
|
|
template<typename Eval> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
unary_operator<prefix_increment>, |
|
actor<Eval> |
|
> |
|
> |
|
operator++(const actor<Eval> &_1) |
|
{ |
|
return compose(unary_operator<prefix_increment>(), _1); |
|
} // end operator++() |
|
|
|
// there's no standard suffix_increment functional, so roll an ad hoc one here |
|
template<typename T> |
|
struct suffix_increment |
|
: public thrust::unary_function<T&,T> |
|
{ |
|
__host__ __device__ T operator()(T &x) const { return x++; } |
|
}; // end suffix_increment |
|
|
|
template<typename Eval> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
unary_operator<suffix_increment>, |
|
actor<Eval> |
|
> |
|
> |
|
operator++(const actor<Eval> &_1, int) |
|
{ |
|
return compose(unary_operator<suffix_increment>(), _1); |
|
} // end operator++() |
|
|
|
// there's no standard prefix_decrement functional, so roll an ad hoc one here |
|
template<typename T> |
|
struct prefix_decrement |
|
: public thrust::unary_function<T&,T&> |
|
{ |
|
__host__ __device__ T& operator()(T &x) const { return --x; } |
|
}; // end prefix_decrement |
|
|
|
template<typename Eval> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
unary_operator<prefix_decrement>, |
|
actor<Eval> |
|
> |
|
> |
|
operator--(const actor<Eval> &_1) |
|
{ |
|
return compose(unary_operator<prefix_decrement>(), _1); |
|
} // end operator--() |
|
|
|
// there's no standard suffix_decrement functional, so roll an ad hoc one here |
|
template<typename T> |
|
struct suffix_decrement |
|
: public thrust::unary_function<T&,T> |
|
{ |
|
__host__ __device__ T operator()(T &x) const { return x--; } |
|
}; // end suffix_decrement |
|
|
|
template<typename Eval> |
|
__host__ __device__ |
|
actor< |
|
composite< |
|
unary_operator<suffix_decrement>, |
|
actor<Eval> |
|
> |
|
> |
|
operator--(const actor<Eval> &_1, int) |
|
{ |
|
return compose(unary_operator<suffix_decrement>(), _1); |
|
} // end operator--() |
|
|
|
} // end functional |
|
} // end detail |
|
} // end thrust |
|
|
|
|