Created
August 10, 2018 12:50
-
-
Save robertmaynard/e1fac8c412da7bd2056df9c07a673561 to your computer and use it in GitHub Desktop.
CUDA 9 fails with local type
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
| /home/robert/Work/local_type/src/main.cu(50): warning: calling a __host__ function from a __host__ __device__ function is not allowed | |
| detected during instantiation of "int64_t vtkm::copy_if(InputIterator, InputIterator, Stencil, OutputIterator, UnaryPredicate) [with InputIterator=thrust::detail::normal_iterator<thrust::device_ptr<float>>, Stencil=thrust::detail::normal_iterator<thrust::device_ptr<uint8_t>>, OutputIterator=thrust::detail::normal_iterator<thrust::device_ptr<float>>, UnaryPredicate=InComplete]" | |
| (73): here | |
| /home/robert/Work/local_type/src/main.cu(70): warning: calling a __host__ function("thrust::device_vector<float, ::thrust::device_malloc_allocator<float> > ::device_vector") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| /home/robert/Work/local_type/src/main.cu(71): warning: calling a __host__ function("thrust::device_vector<unsigned char, ::thrust::device_malloc_allocator<unsigned char> > ::device_vector") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| /home/robert/Work/local_type/src/main.cu(73): warning: calling a __host__ function("thrust::detail::vector_base<float, ::thrust::device_malloc_allocator<float> > ::begin") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| /home/robert/Work/local_type/src/main.cu(73): warning: calling a __host__ function("thrust::detail::vector_base<float, ::thrust::device_malloc_allocator<float> > ::end") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| /home/robert/Work/local_type/src/main.cu(73): warning: calling a __host__ function("thrust::detail::vector_base<unsigned char, ::thrust::device_malloc_allocator<unsigned char> > ::begin") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| /home/robert/Work/local_type/src/main.cu(73): warning: calling a __host__ function("thrust::detail::vector_base<float, ::thrust::device_malloc_allocator<float> > ::begin") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| /home/robert/Work/local_type/src/main.cu(75): warning: calling a __host__ function("thrust::device_vector<unsigned char, ::thrust::device_malloc_allocator<unsigned char> > ::~device_vector") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| /home/robert/Work/local_type/src/main.cu(75): warning: calling a __host__ function("thrust::device_vector<float, ::thrust::device_malloc_allocator<float> > ::~device_vector") from a __host__ __device__ function("Task::operator () const") is not allowed | |
| In file included from tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:1:0: | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:8:311: error: template argument 2 is invalid | |
| typedef thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE; | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:8:325: error: template argument 4 is invalid | |
| typedef thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE; | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:8:343: error: expected initializer before ‘_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE’ | |
| typedef thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE; | |
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | |
| In file included from tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:1:0: | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:27:148: error: variable or field ‘__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_’ declared void | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&, size_t, int *); | |
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:27:148: error: ‘_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE’ was not declared in this scope | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:27:337: error: expected primary-expression before ‘,’ token | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&, size_t, int *); | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:27:345: error: expected primary-expression before ‘,’ token | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&, size_t, int *); | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:27:347: error: expected primary-expression before ‘int’ | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&, size_t, int *); | |
| ^~~ | |
| In file included from tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:1:0: | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:48:148: error: variable or field ‘__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_’ declared void | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&__par0, size_t __par1, int *__par2){__cudaLaunchPrologue(3);__cudaSetupArg(__par0, 0UL);__cudaSetupArgSimple(__par1, 8UL);__cudaSetupArgSimple(__par2, 16UL);__cudaLaunch(((char *)((void ( *)(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE, size_t, int *))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , unsigned long, int *> )));}namespace thrust{ | |
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:48:148: error: ‘_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE’ was not declared in this scope | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:48:337: error: ‘__par0’ was not declared in this scope | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&__par0, size_t __par1, int *__par2){__cudaLaunchPrologue(3);__cudaSetupArg(__par0, 0UL);__cudaSetupArgSimple(__par1, 8UL);__cudaSetupArgSimple(__par2, 16UL);__cudaLaunch(((char *)((void ( *)(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE, size_t, int *))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , unsigned long, int *> )));}namespace thrust{ | |
| ^~~~~~ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:48:337: note: suggested alternative: ‘__hadd’ | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&__par0, size_t __par1, int *__par2){__cudaLaunchPrologue(3);__cudaSetupArg(__par0, 0UL);__cudaSetupArgSimple(__par1, 8UL);__cudaSetupArgSimple(__par2, 16UL);__cudaLaunch(((char *)((void ( *)(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE, size_t, int *))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , unsigned long, int *> )));}namespace thrust{ | |
| ^~~~~~ | |
| __hadd | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:48:352: error: expected primary-expression before ‘__par1’ | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&__par0, size_t __par1, int *__par2){__cudaLaunchPrologue(3);__cudaSetupArg(__par0, 0UL);__cudaSetupArgSimple(__par1, 8UL);__cudaSetupArgSimple(__par2, 16UL);__cudaLaunch(((char *)((void ( *)(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE, size_t, int *))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , unsigned long, int *> )));}namespace thrust{ | |
| ^~~~~~ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:48:360: error: expected primary-expression before ‘int’ | |
| static void __device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE&__par0, size_t __par1, int *__par2){__cudaLaunchPrologue(3);__cudaSetupArg(__par0, 0UL);__cudaSetupArgSimple(__par1, 8UL);__cudaSetupArgSimple(__par2, 16UL);__cudaLaunch(((char *)((void ( *)(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE, size_t, int *))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , unsigned long, int *> )));}namespace thrust{ | |
| ^~~ | |
| In file included from tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:1:0: | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:494: error: template argument 2 is invalid | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:508: error: template argument 4 is invalid | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:544: error: template-id ‘__wrapper__device_stub__kernel_agent<thrust::cuda_cub::__copy_if::InitAgent<thrust::cuda_cub::cub::ScanTileState<int, true>, int*, int>, <expression error>, size_t, int*>’ used as a declarator | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:544: error: variable or field ‘__wrapper__device_stub__kernel_agent’ declared void | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:544: error: ‘_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE’ was not declared in this scope | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:734: error: ‘__cuda_0’ was not declared in this scope | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^~~~~~~~ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:734: note: suggested alternative: ‘__caddr_t’ | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^~~~~~~~ | |
| __caddr_t | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:752: error: expected primary-expression before ‘&’ token | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:753: error: ‘__cuda_1’ was not declared in this scope | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^~~~~~~~ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:753: note: suggested alternative: ‘__caddr_t’ | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^~~~~~~~ | |
| __caddr_t | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:52:762: error: expected primary-expression before ‘int’ | |
| template<> __specialization_static void __wrapper__device_stub__kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::__copy_if::CopyIfAgent< ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<unsigned char> > , ::thrust::detail::normal_iterator< ::thrust::device_ptr<float> > , ::vtkm::WrappedUnaryPredicate<unsigned char, ::> , int, int *> ::ScanTileState, ::size_t,int *>( _ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &__cuda_0,::size_t &__cuda_1,int *&__cuda_2){__device_stub__ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_( (_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE &)__cuda_0,(::size_t &)__cuda_1,(int *&)__cuda_2);}}}} | |
| ^~~ | |
| In file included from /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:5:0, | |
| from tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:1: | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c: In function ‘void __nv_cudaEntityRegisterCallback(void**)’: | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:68:3482: error: expected primary-expression before ‘void’ | |
| static void __nv_cudaEntityRegisterCallback(void **__T1167){__nv_dummy_param_ref(__T1167);__nv_save_fatbinhandle_for_managed_rt(__T1167);__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub11__transform17unary_transform_fINS_10device_ptrIfEES4_NS1_14no_stencil_tagENS_8identityIfEENS1_21always_true_predicateEEE, _ZN6thrust15iterator_traitsINS_10device_ptrIfEEE15difference_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__transform::unary_transform_f< ::thrust::device_ptr<float> , ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> , ::thrust::cuda_cub::__transform::unary_transform_f< ::thrust::device_ptr<float> , ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_11__transform17unary_transform_fINS_10device_ptrIfEES8_NS5_14no_stencil_tagENS_8identityIfEENS5_21always_true_predicateEEElEESD_lEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub11__transform17unary_transform_fIPiS3_NS1_14no_stencil_tagENS_8identityIiEENS1_21always_true_predicateEEE, _ZN6thrust15iterator_traitsIPiE15difference_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__transform::unary_transform_f<int *, int *, ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<int> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> , ::thrust::cuda_cub::__transform::unary_transform_f<int *, int *, ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<int> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_11__transform17unary_transform_fIPiS7_NS5_14no_stencil_tagENS_8identityIiEENS5_21always_true_predicateEEElEESC_lEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub11__transform17unary_transform_fIPKfNS_10device_ptrIfEENS1_14no_stencil_tagENS_8identityIfEENS1_21always_true_predicateEEE, _ZN6thrust15iterator_traitsIPKfE15difference_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__transform::unary_transform_f<const float *, ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> , ::thrust::cuda_cub::__transform::unary_transform_f<const float *, ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_11__transform17unary_transform_fIPKfNS_10device_ptrIfEENS5_14no_stencil_tagENS_8identityIfEENS5_21always_true_predicateEEElEESF_lEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE, size_t, int *))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , unsigned long, int *> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_, ( ::thrust::cuda_cub::__copy_if::PtxPolicy<(int)128, (int)1, (int)1, ( ::thrust::cuda_cub::cub::BlockLoadAlgorithm)0, ( ::thrust::cuda_cub::cub::CacheLoadModifier)5, ( ::thrust::cuda_cub::cub::BlockScanAlgorithm)2> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub20__uninitialized_fill7functorINS_10device_ptrIhEEhEE, _ZN6thrust6detail18contiguous_storageIhNS_23device_malloc_allocatorIhEEE9size_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<unsigned char> , unsigned char> , unsigned long> , ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<unsigned char> , unsigned char> , unsigned long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_20__uninitialized_fill7functorINS_10device_ptrIhEEhEEmEES9_mEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub20__uninitialized_fill7functorINS_10device_ptrIfEEfEE, _ZN6thrust6detail18contiguous_storageIfNS_23device_malloc_allocatorIfEEE9size_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<float> , float> , unsigned long> , ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<float> , float> , unsigned long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_20__uninitialized_fill7functorINS_10device_ptrIfEEfEEmEES9_mEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)(void))thrust::cuda_cub::cub::EmptyKernel<void> ), _ZN6thrust8cuda_cub3cub11EmptyKernelIvEEvv, (-1));__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust6system6detail10sequential3seqE,::thrust::system::detail::sequential::seq), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust8cuda_cub3parE,::thrust::cuda_cub::par), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_1E,::thrust::placeholders::_1), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_2E,::thrust::placeholders::_2), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_3E,::thrust::placeholders::_3), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_4E,::thrust::placeholders::_4), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_5E,::thrust::placeholders::_5), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_6E,::thrust::placeholders::_6), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_7E,::thrust::placeholders::_7), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_8E,::thrust::placeholders::_8), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_9E,::thrust::placeholders::_9), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders3_10E,::thrust::placeholders::_10), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust3seqE,::thrust::seq), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust6deviceE,::thrust::device), 0, 1UL, 0, 0);} | |
| ^ | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:68:3482: error: expected ‘)’ before ‘void’ | |
| In file included from tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:1:0: | |
| /tmp/tmpxft_00003e1e_00000000-5_main.cudafe1.stub.c:68:0: error: expected ‘)’ before ‘;’ token | |
| static void __nv_cudaEntityRegisterCallback(void **__T1167){__nv_dummy_param_ref(__T1167);__nv_save_fatbinhandle_for_managed_rt(__T1167);__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub11__transform17unary_transform_fINS_10device_ptrIfEES4_NS1_14no_stencil_tagENS_8identityIfEENS1_21always_true_predicateEEE, _ZN6thrust15iterator_traitsINS_10device_ptrIfEEE15difference_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__transform::unary_transform_f< ::thrust::device_ptr<float> , ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> , ::thrust::cuda_cub::__transform::unary_transform_f< ::thrust::device_ptr<float> , ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_11__transform17unary_transform_fINS_10device_ptrIfEES8_NS5_14no_stencil_tagENS_8identityIfEENS5_21always_true_predicateEEElEESD_lEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub11__transform17unary_transform_fIPiS3_NS1_14no_stencil_tagENS_8identityIiEENS1_21always_true_predicateEEE, _ZN6thrust15iterator_traitsIPiE15difference_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__transform::unary_transform_f<int *, int *, ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<int> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> , ::thrust::cuda_cub::__transform::unary_transform_f<int *, int *, ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<int> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_11__transform17unary_transform_fIPiS7_NS5_14no_stencil_tagENS_8identityIiEENS5_21always_true_predicateEEElEESC_lEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub11__transform17unary_transform_fIPKfNS_10device_ptrIfEENS1_14no_stencil_tagENS_8identityIfEENS1_21always_true_predicateEEE, _ZN6thrust15iterator_traitsIPKfE15difference_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__transform::unary_transform_f<const float *, ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> , ::thrust::cuda_cub::__transform::unary_transform_f<const float *, ::thrust::device_ptr<float> , ::thrust::cuda_cub::__transform::no_stencil_tag, ::thrust::identity<float> , ::thrust::cuda_cub::__transform::always_true_predicate> , long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_11__transform17unary_transform_fIPKfNS_10device_ptrIfEENS5_14no_stencil_tagENS_8identityIfEENS5_21always_true_predicateEEElEESF_lEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)(_ZN6thrust8cuda_cub9__copy_if11CopyIfAgentINS_6detail15normal_iteratorINS_10device_ptrIfEEEENS4_INS5_IhEEEES7_N4vtkm21WrappedUnaryPredicateIhZNK4TaskclEvE10InCompleteEEiPiE13ScanTileStateE, size_t, int *))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__copy_if::InitAgent< ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , int *, int> , ::thrust::cuda_cub::cub::ScanTileState<int, (bool)1> , unsigned long, int *> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_9__copy_if9InitAgentINS0_3cub13ScanTileStateIiLb1EEEPiiEES7_mS8_EEvT0_T1_T2_, ( ::thrust::cuda_cub::__copy_if::PtxPolicy<(int)128, (int)1, (int)1, ( ::thrust::cuda_cub::cub::BlockLoadAlgorithm)0, ( ::thrust::cuda_cub::cub::CacheLoadModifier)5, ( ::thrust::cuda_cub::cub::BlockScanAlgorithm)2> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub20__uninitialized_fill7functorINS_10device_ptrIhEEhEE, _ZN6thrust6detail18contiguous_storageIhNS_23device_malloc_allocatorIhEEE9size_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<unsigned char> , unsigned char> , unsigned long> , ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<unsigned char> , unsigned char> , unsigned long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_20__uninitialized_fill7functorINS_10device_ptrIhEEhEEmEES9_mEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)( _ZN6thrust8cuda_cub20__uninitialized_fill7functorINS_10device_ptrIfEEfEE, _ZN6thrust6detail18contiguous_storageIfNS_23device_malloc_allocatorIfEEE9size_typeE))thrust::cuda_cub::core::_kernel_agent< ::thrust::cuda_cub::__parallel_for::ParallelForAgent< ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<float> , float> , unsigned long> , ::thrust::cuda_cub::__uninitialized_fill::functor< ::thrust::device_ptr<float> , float> , unsigned long> ), _ZN6thrust8cuda_cub4core13_kernel_agentINS0_14__parallel_for16ParallelForAgentINS0_20__uninitialized_fill7functorINS_10device_ptrIfEEfEEmEES9_mEEvT0_T1_, ( ::thrust::cuda_cub::__parallel_for::PtxPolicy<(int)256, (int)2, (int)1> ::BLOCK_THREADS));__cudaRegisterEntry(__T1167, ((void ( *)(void))thrust::cuda_cub::cub::EmptyKernel<void> ), _ZN6thrust8cuda_cub3cub11EmptyKernelIvEEvv, (-1));__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust6system6detail10sequential3seqE,::thrust::system::detail::sequential::seq), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust8cuda_cub3parE,::thrust::cuda_cub::par), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_1E,::thrust::placeholders::_1), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_2E,::thrust::placeholders::_2), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_3E,::thrust::placeholders::_3), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_4E,::thrust::placeholders::_4), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_5E,::thrust::placeholders::_5), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_6E,::thrust::placeholders::_6), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_7E,::thrust::placeholders::_7), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_8E,::thrust::placeholders::_8), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders2_9E,::thrust::placeholders::_9), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust12placeholders3_10E,::thrust::placeholders::_10), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust3seqE,::thrust::seq), 0, 1UL, 0, 0);__cudaRegisterVariable(__T1167, __shadow_var(_ZN57_INTERNAL_39_tmpxft_00003e1e_00000000_6_main_cpp1_ii_main6thrust6deviceE,::thrust::device), 0, 1UL, 0, 0);} | |
| make[2]: *** [CMakeFiles/errors.dir/main.cu.o] Error 1 | |
| make[1]: *** [CMakeFiles/errors.dir/all] Error 2 | |
| make: *** [all] Error 2 |
This file contains bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
| #include <thrust/copy.h> | |
| #include <thrust/distance.h> | |
| #include <thrust/execution_policy.h> | |
| #include <thrust/system/cuda/execution_policy.h> | |
| #include <thrust/system/cuda/memory.h> | |
| /// Binary Predicate that takes two arguments argument \c x, and \c y and | |
| /// returns True if and only if \c x is equal to \c y. | |
| /// Note: Requires Type \p T implement the == operator. | |
| struct InCompleteWhichWorks { | |
| __device__ bool operator()(const std::uint8_t &complete) const { | |
| return !complete; | |
| } | |
| }; | |
| namespace vtkm { | |
| // Unary function object wrapper which can detect and handle calling the | |
| // wrapped operator with complex value types such as | |
| // PortalValue which happen when passed an input array that | |
| // is implicit. | |
| template <typename T_, typename Function> struct WrappedUnaryPredicate { | |
| using T = typename std::remove_const<T_>::type; | |
| // make typedefs that thust expects unary operators to have | |
| using first_argument_type = T; | |
| using result_type = bool; | |
| Function m_f; | |
| __device__ WrappedUnaryPredicate() : m_f() {} | |
| __host__ WrappedUnaryPredicate(const Function &f) : m_f(f) {} | |
| __device__ bool operator()(const T &x) const { return m_f(x); } | |
| __device__ bool operator()(const T *x) const { return m_f(*x); } | |
| }; | |
| template <typename InputIterator, typename Stencil, typename OutputIterator, | |
| typename UnaryPredicate> | |
| __host__ __device__ static std::int64_t | |
| copy_if(InputIterator valuesBegin, InputIterator valuesEnd, Stencil stencil, | |
| OutputIterator outputBegin, UnaryPredicate unary_predicate) { | |
| using ValueType = typename Stencil::value_type; | |
| vtkm::WrappedUnaryPredicate<ValueType, UnaryPredicate> up(unary_predicate); | |
| auto newLast = | |
| ::thrust::copy_if(::thrust::cuda::par.on(cudaStreamPerThread), | |
| valuesBegin, valuesEnd, stencil, outputBegin, up); | |
| return static_cast<std::int64_t>(::thrust::distance(outputBegin, newLast)); | |
| } | |
| } // namespace vtkm | |
| struct Task { | |
| __host__ __device__ bool operator()() const { | |
| struct InComplete { | |
| __device__ bool operator()(std::uint8_t complete) const { | |
| return !complete; | |
| } | |
| }; | |
| thrust::device_vector<float> points(500); | |
| thrust::device_vector<std::uint8_t> stencil(500); | |
| auto size = vtkm::copy_if(points.begin(), points.end(), stencil.begin(), | |
| points.begin(), InComplete()); | |
| return size > 0; | |
| } | |
| }; | |
| int main(int argc, char **) { | |
| Task t; | |
| return t() ? 0 : 1; | |
| } |
Sign up for free
to join this conversation on GitHub.
Already have an account?
Sign in to comment