/* * 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 THRUST_NAMESPACE_BEGIN namespace system { namespace detail { namespace generic { namespace detail { template _CCCL_HOST_DEVICE void uninitialized_fill( thrust::execution_policy& exec, ForwardIterator first, ForwardIterator last, const T& x, thrust::detail::true_type) // ::cuda::std::is_trivially_copy_constructible { thrust::fill(exec, first, last, x); } // end uninitialized_fill() template _CCCL_HOST_DEVICE void uninitialized_fill( thrust::execution_policy& exec, ForwardIterator first, ForwardIterator last, const T& x, thrust::detail::false_type) // ::cuda::std::is_trivially_copy_constructible { typedef typename iterator_traits::value_type ValueType; thrust::for_each(exec, first, last, thrust::detail::uninitialized_fill_functor(x)); } // end uninitialized_fill() template _CCCL_HOST_DEVICE ForwardIterator uninitialized_fill_n( thrust::execution_policy& exec, ForwardIterator first, Size n, const T& x, thrust::detail::true_type) // ::cuda::std::is_trivially_copy_constructible { return thrust::fill_n(exec, first, n, x); } // end uninitialized_fill() template _CCCL_HOST_DEVICE ForwardIterator uninitialized_fill_n( thrust::execution_policy& exec, ForwardIterator first, Size n, const T& x, thrust::detail::false_type) // ::cuda::std::is_trivially_copy_constructible { typedef typename iterator_traits::value_type ValueType; return thrust::for_each_n(exec, first, n, thrust::detail::uninitialized_fill_functor(x)); } // end uninitialized_fill() } // namespace detail template _CCCL_HOST_DEVICE void uninitialized_fill( thrust::execution_policy& exec, ForwardIterator first, ForwardIterator last, const T& x) { typedef typename iterator_traits::value_type ValueType; typedef ::cuda::std::is_trivially_copy_constructible ValueTypeHasTrivialCopyConstructor; thrust::system::detail::generic::detail::uninitialized_fill( exec, first, last, x, ValueTypeHasTrivialCopyConstructor()); } // end uninitialized_fill() template _CCCL_HOST_DEVICE ForwardIterator uninitialized_fill_n(thrust::execution_policy& exec, ForwardIterator first, Size n, const T& x) { typedef typename iterator_traits::value_type ValueType; typedef ::cuda::std::is_trivially_copy_constructible ValueTypeHasTrivialCopyConstructor; return thrust::system::detail::generic::detail::uninitialized_fill_n( exec, first, n, x, ValueTypeHasTrivialCopyConstructor()); } // end uninitialized_fill() } // end namespace generic } // end namespace detail } // end namespace system THRUST_NAMESPACE_END