{"action":"created","issue":{"url":"https://api.github.com/repos/psychocoderHPC/piconalpaka/issues/13","labels_url":"https://api.github.com/repos/psychocoderHPC/piconalpaka/issues/13/labels{/name}","comments_url":"https://api.github.com/repos/psychocoderHPC/piconalpaka/issues/13/comments","events_url":"https://api.github.com/repos/psychocoderHPC/piconalpaka/issues/13/events","html_url":"https://github.com/psychocoderHPC/piconalpaka/issues/13","id":112759297,"number":13,"title":"CUDA Acc laserwakefield example std::runtime_error","user":{"login":"erikzenker","id":341041,"avatar_url":"https://avatars.githubusercontent.com/u/341041?v=3","gravatar_id":"","url":"https://api.github.com/users/erikzenker","html_url":"https://github.com/erikzenker","followers_url":"https://api.github.com/users/erikzenker/followers","following_url":"https://api.github.com/users/erikzenker/following{/other_user}","gists_url":"https://api.github.com/users/erikzenker/gists{/gist_id}","starred_url":"https://api.github.com/users/erikzenker/starred{/owner}{/repo}","subscriptions_url":"https://api.github.com/users/erikzenker/subscriptions","organizations_url":"https://api.github.com/users/erikzenker/orgs","repos_url":"https://api.github.com/users/erikzenker/repos","events_url":"https://api.github.com/users/erikzenker/events{/privacy}","received_events_url":"https://api.github.com/users/erikzenker/received_events","type":"User","site_admin":false},"labels":[{"url":"https://api.github.com/repos/psychocoderHPC/piconalpaka/labels/bug","name":"bug","color":"fc2929"}],"state":"open","locked":false,"assignee":null,"milestone":null,"comments":8,"created_at":"2015-10-22T08:53:55Z","updated_at":"2015-10-28T09:34:54Z","closed_at":null,"body":"Following error in the beginning of the execution:\r\n\r\n    [1,0]<stderr>:terminate called after throwing an instance of 'std::runtime_error'\r\n    [1,0]<stderr>:  what():  Unexpected return value 'an illegal memory access was encountered'from cudaEventQuery!\r\n\r\nError does not occur when the [species init pipeline](https://github.com/psychocoderHPC/piconalpaka/blob/devAlpaka/examples/LaserWakefield/include/simulation_defines/param/speciesInitialization.param#L85-L99) is empy.\r\n\r\nDebuging the problem with cuda-gdb delivers the following output:\r\n\r\n    CUDA Exception: Warp Out-of-range Address\r\n    Program received signal CUDA_EXCEPTION_5, Warp Out-of-range Address.\r\n    [Switching focus to CUDA kernel 0, grid 868, block (0,3,0), thread (0,0,2), device 0, sm 0, warp 4, lane 0]\r\n    void alpaka::exec::cuda::detail::cudaKernel<std::integral_constant<unsigned long, 3ul>, int, picongpu::KernelMoveAndMarkParticles<PMacc::SuperCellDescription<PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, PMacc::math::CT::Int<1, 1, 1>, PMacc::math::CT::Int<2, 2, 2> > >, PMacc::ParticlesBox<PMacc::Frame<PMacc::ParticlesBuffer<PMacc::ParticleDescription<boost::mpl::string<101, 0, 0, 0, 0, 0, 0, 0>, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, boost::mpl::v_item<picongpu::placeholder_definition11::weighting, boost::mpl::v_item<picongpu::placeholder_definition9::momentum, boost::mpl::v_item<picongpu::placeholder_definition6::position<picongpu::placeholder_definition8::position_pic, PMacc::placeholder_definition5::pmacc_isAlias>, boost::mpl::vector0<mpl_::na>, 0>, 0>, 0>, boost::mpl::vector<picongpu::placeholder_definition16::particlePusher<picongpu::particles::pusher::Boris, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition15::shape<picongpu::particles::shapes::TSC, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition18::interpolation<picongpu::FieldToParticleInterpolation<picongpu::particles::shapes::TSC, picongpu::AssignedTrilinearInterpolation>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition19::current<picongpu::currentSolver::Esirkepov<picongpu::particles::shapes::TSC, 3u>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition21::massRatio<picongpu::placeholder_definition24::MassRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition22::chargeRatio<picongpu::placeholder_definition25::ChargeRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na>, picongpu::CommunicationId<0u>, boost::mpl::vector0<mpl_::na> >, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, 3u>::OperatorCreatePairStaticArray<256u>, PMacc::ParticleDescription<boost::mpl::string<101, 0, 0, 0, 0, 0, 0, 0>, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, boost::mpl::v_item<PMacc::placeholder_definition3::multiMask, boost::mpl::v_item<PMacc::placeholder_definition2::localCellIdx, boost::mpl::v_item<picongpu::placeholder_definition11::weighting, boost::mpl::v_item<picongpu::placeholder_definition9::momentum, boost::mpl::v_item<picongpu::placeholder_definition6::position<picongpu::placeholder_definition8::position_pic, PMacc::placeholder_definition5::pmacc_isAlias>, boost::mpl::vector0<mpl_::na>, 0>, 0>, 0>, 0>, 0>, boost::mpl::vector<picongpu::placeholder_definition16::particlePusher<picongpu::particles::pusher::Boris, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition15::shape<picongpu::particles::shapes::TSC, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition18::interpolation<picongpu::FieldToParticleInterpolation<picongpu::particles::shapes::TSC, picongpu::AssignedTrilinearInterpolation>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition19::current<picongpu::currentSolver::Esirkepov<picongpu::particles::shapes::TSC, 3u>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition21::massRatio<picongpu::placeholder_definition24::MassRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition22::chargeRatio<picongpu::placeholder_definition25::ChargeRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na>, boost::mpl::vector1<picongpu::CommunicationId<0u> >, boost::mpl::v_item<PMacc::NextFramePtr<mpl_::arg<1> >, boost::mpl::v_item<PMacc::PreviousFramePtr<mpl_::arg<1> >, boost::mpl::vector0<mpl_::na>, 0>, 0> > >, 3u>, PMacc::DataBox<PMacc::PitchedBox<PMacc::math::Vector<float, 3, PMacc::math::StandardAccessor, PMacc::math::StandardNavigator, PMacc::math::detail::Vector_components>, 3u> >, PMacc::DataBox<PMacc::PitchedBox<PMacc::math::Vector<float, 3, PMacc::math::StandardAccessor, PMacc::math::StandardNavigator, PMacc::math::detail::Vector_components>, 3u> >, picongpu::PushParticlePerFrame<picongpu::particlePusherBoris::Push<picongpu::Velocity, picongpu::Gamma<float> >, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, picongpu::FieldToParticleInterpolation<picongpu::particles::shapes::TSC, picongpu::AssignedTrilinearInterpolation>, picongpu::yeeCell::YeeCell>, PMacc::AreaMapping<3u, PMacc::MappingDescription<3u, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> > > > >(alpaka::Vec<std::integral_constant<unsigned long, 3ul>, int>, picongpu::KernelMoveAndMarkParticles<PMacc::SuperCellDescription<PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, PMacc::math::CT::Int<1, 1, 1>, PMacc::math::CT::Int<2, 2, 2> > >, PMacc::ParticlesBox<PMacc::Frame<PMacc::ParticlesBuffer<PMacc::ParticleDescription<boost::mpl::string<101, 0, 0, 0, 0, 0, 0, 0>, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, boost::mpl::v_item<picongpu::placeholder_definition11::weighting, boost::mpl::v_item<picongpu::placeholder_definition9::momentum, boost::mpl::v_item<picongpu::placeholder_definition6::position<picongpu::placeholder_definition8::position_pic, PMacc::placeholder_definition5::pmacc_isAlias>, boost::mpl::vector0<mpl_::na>, 0>, 0>, 0>, boost::mpl::vector<picongpu::placeholder_definition16::particlePusher<picongpu::particles::pusher::Boris, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition15::shape<picongpu::particles::shapes::TSC, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition18::interpolation<picongpu::FieldToParticleInterpolation<picongpu::particles::shapes::TSC, picongpu::AssignedTrilinearInterpolation>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition19::current<picongpu::currentSolver::Esirkepov<picongpu::particles::shapes::TSC, 3u>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition21::massRatio<picongpu::placeholder_definition24::MassRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition22::chargeRatio<picongpu::placeholder_definition25::ChargeRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na>, picongpu::CommunicationId<0u>, boost::mpl::vector0<mpl_::na> >, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, 3u>::OperatorCreatePairStaticArray<256u>, PMacc::ParticleDescription<boost::mpl::string<101, 0, 0, 0, 0, 0, 0, 0>, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, boost::mpl::v_item<PMacc::placeholder_definition3::multiMask, boost::mpl::v_item<PMacc::placeholder_definition2::localCellIdx, boost::mpl::v_item<picongpu::placeholder_definition11::weighting, boost::mpl::v_item<picongpu::placeholder_definition9::momentum, boost::mpl::v_item<picongpu::placeholder_definition6::position<picongpu::placeholder_definition8::position_pic, PMacc::placeholder_definition5::pmacc_isAlias>, boost::mpl::vector0<mpl_::na>, 0>, 0>, 0>, 0>, 0>, boost::mpl::vector<picongpu::placeholder_definition16::particlePusher<picongpu::particles::pusher::Boris, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition15::shape<picongpu::particles::shapes::TSC, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition18::interpolation<picongpu::FieldToParticleInterpolation<picongpu::particles::shapes::TSC, picongpu::AssignedTrilinearInterpolation>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition19::current<picongpu::currentSolver::Esirkepov<picongpu::particles::shapes::TSC, 3u>, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition21::massRatio<picongpu::placeholder_definition24::MassRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, picongpu::placeholder_definition22::chargeRatio<picongpu::placeholder_definition25::ChargeRatioElectrons, PMacc::placeholder_definition5::pmacc_isAlias>, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na, mpl_::na>, boost::mpl::vector1<picongpu::CommunicationId<0u> >, boost::mpl::v_item<PMacc::NextFramePtr<mpl_::arg<1> >, boost::mpl::v_item<PMacc::PreviousFramePtr<mpl_::arg<1> >, boost::mpl::vector0<mpl_::na>, 0>, 0> > >, 3u>, PMacc::DataBox<PMacc::PitchedBox<PMacc::math::Vector<float, 3, PMacc::math::StandardAccessor, PMacc::math::StandardNavigator, PMacc::math::detail::Vector_components>, 3u> >, PMacc::DataBox<PMacc::PitchedBox<PMacc::math::Vector<float, 3, PMacc::math::StandardAccessor, PMacc::math::StandardNavigator, PMacc::math::detail::Vector_components>, 3u> >, picongpu::PushParticlePerFrame<picongpu::particlePusherBoris::Push<picongpu::Velocity, picongpu::Gamma<float> >, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> >, picongpu::FieldToParticleInterpolation<picongpu::particles::shapes::TSC, picongpu::AssignedTrilinearInterpolation>, picongpu::yeeCell::YeeCell>, PMacc::AreaMapping<3u, PMacc::MappingDescription<3u, PMacc::math::CT::Vector<mpl_::integral_c<int, 8>, mpl_::integral_c<int, 8>, mpl_::integral_c<int, 4> > > >)<<<(4,4,8),(8,8,4)>>> ()\r\n\r\nI continue to debug the error and keep tracking my steps here."},"comment":{"url":"https://api.github.com/repos/psychocoderHPC/piconalpaka/issues/comments/151780187","html_url":"https://github.com/psychocoderHPC/piconalpaka/issues/13#issuecomment-151780187","issue_url":"https://api.github.com/repos/psychocoderHPC/piconalpaka/issues/13","id":151780187,"user":{"login":"psychocoderHPC","id":4037125,"avatar_url":"https://avatars.githubusercontent.com/u/4037125?v=3","gravatar_id":"","url":"https://api.github.com/users/psychocoderHPC","html_url":"https://github.com/psychocoderHPC","followers_url":"https://api.github.com/users/psychocoderHPC/followers","following_url":"https://api.github.com/users/psychocoderHPC/following{/other_user}","gists_url":"https://api.github.com/users/psychocoderHPC/gists{/gist_id}","starred_url":"https://api.github.com/users/psychocoderHPC/starred{/owner}{/repo}","subscriptions_url":"https://api.github.com/users/psychocoderHPC/subscriptions","organizations_url":"https://api.github.com/users/psychocoderHPC/orgs","repos_url":"https://api.github.com/users/psychocoderHPC/repos","events_url":"https://api.github.com/users/psychocoderHPC/events{/privacy}","received_events_url":"https://api.github.com/users/psychocoderHPC/received_events","type":"User","site_admin":false},"created_at":"2015-10-28T09:34:54Z","updated_at":"2015-10-28T09:34:54Z","body":"did you rebased your alpka against the latest shared mem fix of alpaka and the same with piconalpaka.\r\nWhat I saw in my last tests is that all kernel used to much stack frame (lmem) what results in `out of memory`"}}