/* * Copyright 2008-2013 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 #if defined(_CCCL_IMPLICIT_SYSTEM_HEADER_GCC) # pragma GCC system_header #elif defined(_CCCL_IMPLICIT_SYSTEM_HEADER_CLANG) # pragma clang system_header #elif defined(_CCCL_IMPLICIT_SYSTEM_HEADER_MSVC) # pragma system_header #endif // no system header #include #include #include #include #include #include #include THRUST_NAMESPACE_BEGIN _CCCL_EXEC_CHECK_DISABLE template _CCCL_HOST_DEVICE typename thrust::iterator_traits::value_type reduce(const thrust::detail::execution_policy_base& exec, InputIterator first, InputIterator last) { using thrust::system::detail::generic::reduce; return reduce(thrust::detail::derived_cast(thrust::detail::strip_const(exec)), first, last); } // end reduce() _CCCL_EXEC_CHECK_DISABLE template _CCCL_HOST_DEVICE T reduce( const thrust::detail::execution_policy_base& exec, InputIterator first, InputIterator last, T init) { using thrust::system::detail::generic::reduce; return reduce(thrust::detail::derived_cast(thrust::detail::strip_const(exec)), first, last, init); } // end reduce() _CCCL_EXEC_CHECK_DISABLE template _CCCL_HOST_DEVICE T reduce( const thrust::detail::execution_policy_base& exec, InputIterator first, InputIterator last, T init, BinaryFunction binary_op) { using thrust::system::detail::generic::reduce; return reduce(thrust::detail::derived_cast(thrust::detail::strip_const(exec)), first, last, init, binary_op); } // end reduce() _CCCL_EXEC_CHECK_DISABLE template _CCCL_HOST_DEVICE thrust::pair reduce_by_key( const thrust::detail::execution_policy_base& exec, InputIterator1 keys_first, InputIterator1 keys_last, InputIterator2 values_first, OutputIterator1 keys_output, OutputIterator2 values_output) { using thrust::system::detail::generic::reduce_by_key; return reduce_by_key( thrust::detail::derived_cast(thrust::detail::strip_const(exec)), keys_first, keys_last, values_first, keys_output, values_output); } // end reduce_by_key() _CCCL_EXEC_CHECK_DISABLE template _CCCL_HOST_DEVICE thrust::pair reduce_by_key( const thrust::detail::execution_policy_base& exec, InputIterator1 keys_first, InputIterator1 keys_last, InputIterator2 values_first, OutputIterator1 keys_output, OutputIterator2 values_output, BinaryPredicate binary_pred) { using thrust::system::detail::generic::reduce_by_key; return reduce_by_key( thrust::detail::derived_cast(thrust::detail::strip_const(exec)), keys_first, keys_last, values_first, keys_output, values_output, binary_pred); } // end reduce_by_key() _CCCL_EXEC_CHECK_DISABLE template _CCCL_HOST_DEVICE thrust::pair reduce_by_key( const thrust::detail::execution_policy_base& exec, InputIterator1 keys_first, InputIterator1 keys_last, InputIterator2 values_first, OutputIterator1 keys_output, OutputIterator2 values_output, BinaryPredicate binary_pred, BinaryFunction binary_op) { using thrust::system::detail::generic::reduce_by_key; return reduce_by_key( thrust::detail::derived_cast(thrust::detail::strip_const(exec)), keys_first, keys_last, values_first, keys_output, values_output, binary_pred, binary_op); } // end reduce_by_key() template typename thrust::iterator_traits::value_type reduce(InputIterator first, InputIterator last) { using thrust::system::detail::generic::select_system; using System = typename thrust::iterator_system::type; System system; return thrust::reduce(select_system(system), first, last); } template T reduce(InputIterator first, InputIterator last, T init) { using thrust::system::detail::generic::select_system; using System = typename thrust::iterator_system::type; System system; return thrust::reduce(select_system(system), first, last, init); } template T reduce(InputIterator first, InputIterator last, T init, BinaryFunction binary_op) { using thrust::system::detail::generic::select_system; using System = typename thrust::iterator_system::type; System system; return thrust::reduce(select_system(system), first, last, init, binary_op); } template thrust::pair reduce_by_key( InputIterator1 keys_first, InputIterator1 keys_last, InputIterator2 values_first, OutputIterator1 keys_output, OutputIterator2 values_output) { using thrust::system::detail::generic::select_system; using System1 = typename thrust::iterator_system::type; using System2 = typename thrust::iterator_system::type; using System3 = typename thrust::iterator_system::type; using System4 = typename thrust::iterator_system::type; System1 system1; System2 system2; System3 system3; System4 system4; return thrust::reduce_by_key( select_system(system1, system2, system3, system4), keys_first, keys_last, values_first, keys_output, values_output); } template thrust::pair reduce_by_key( InputIterator1 keys_first, InputIterator1 keys_last, InputIterator2 values_first, OutputIterator1 keys_output, OutputIterator2 values_output, BinaryPredicate binary_pred) { using thrust::system::detail::generic::select_system; using System1 = typename thrust::iterator_system::type; using System2 = typename thrust::iterator_system::type; using System3 = typename thrust::iterator_system::type; using System4 = typename thrust::iterator_system::type; System1 system1; System2 system2; System3 system3; System4 system4; return thrust::reduce_by_key( select_system(system1, system2, system3, system4), keys_first, keys_last, values_first, keys_output, values_output, binary_pred); } template thrust::pair reduce_by_key( InputIterator1 keys_first, InputIterator1 keys_last, InputIterator2 values_first, OutputIterator1 keys_output, OutputIterator2 values_output, BinaryPredicate binary_pred, BinaryFunction binary_op) { using thrust::system::detail::generic::select_system; using System1 = typename thrust::iterator_system::type; using System2 = typename thrust::iterator_system::type; using System3 = typename thrust::iterator_system::type; using System4 = typename thrust::iterator_system::type; System1 system1; System2 system2; System3 system3; System4 system4; return thrust::reduce_by_key( select_system(system1, system2, system3, system4), keys_first, keys_last, values_first, keys_output, values_output, binary_pred, binary_op); } THRUST_NAMESPACE_END