This bugzilla service is closed. All entries have been migrated to https://gitlab.com/libeigen/eigen
Bug 1415 - Cuda: Calling some Eigen methods failing with Address 0x00000000 is out of bounds
Summary: Cuda: Calling some Eigen methods failing with Address 0x00000000 is out of bo...
Status: NEW
Alias: None
Product: Eigen
Classification: Unclassified
Component: Core - general (show other bugs)
Version: 3.3 (current stable)
Hardware: GPU (CUDA) Linux
: Normal Crash
Assignee: Nobody
URL:
Whiteboard:
Keywords:
Depends on:
Blocks:
 
Reported: 2017-04-18 19:26 UTC by Ali Nakipoglu
Modified: 2019-12-04 16:56 UTC (History)
3 users (show)



Attachments
Test Project Directory (25.77 KB, application/x-gzip)
2017-04-18 19:26 UTC, Ali Nakipoglu
no flags Details

Description Ali Nakipoglu 2017-04-18 19:26:00 UTC
Created attachment 784 [details]
Test Project Directory

Hi,

For decomposing/composing transform matrices in Cuda kernels, I am using Transform primitive and calling Transform<>::fromPositionOrientationScale or Transform<>::computeRotationScaling causing my application to freeze. Running Cuda-Memcheck report prints:

========= CUDA-MEMCHECK
========= Invalid __global__ read of size 4
=========     at 0x00000050 in kernel(unsigned long, Eigen::Matrix<float, int=4, int=4, int=2, int=4, int=4>*)
=========     by thread (0,0,0) in block (0,0,0)
=========     Address 0x00000000 is out of bounds
=========     Saved host backtrace up to driver entry point at kernel launch time
=========     Host Frame:/usr/lib64/libcuda.so.1 (cuLaunchKernel + 0x2c5) [0x204235]
=========     Host Frame:libcudart.so.8.0 [0xd23d]
=========     Host Frame:libcudart.so.8.0 (cudaLaunch + 0x143) [0x33783]
=========     Host Frame:EigenTest [0xf4d]
=========     Host Frame:EigenTest (_Z63__device_stub__Z6kernelmPN5Eigen6MatrixIfLi4ELi4ELi2ELi4ELi4EEEmPN5Eigen6MatrixIfLi4ELi4ELi2ELi4ELi4EEE + 0x67) [0xe53]
=========     Host Frame:EigenTest (_Z6kernelmPN5Eigen6MatrixIfLi4ELi4ELi2ELi4ELi4EEE + 0x23) [0xe7e]
=========     Host Frame:EigenTest (_Z4testv + 0x91) [0xd86]
=========     Host Frame:EigenTest (main + 0x9) [0xcd9]
=========     Host Frame:/lib64/libc.so.6 (__libc_start_main + 0xfd) [0x1ed1d]
=========     Host Frame:EigenTest [0xc09]
=========
========= Program hit cudaErrorLaunchFailure (error 4) due to "unspecified launch failure" on CUDA API call to cudaDeviceSynchronize. 
=========     Saved host backtrace up to driver entry point at error
=========     Host Frame:/usr/lib64/libcuda.so.1 [0x2ef503]
=========     Host Frame:libcudart.so.8.0 (cudaDeviceSynchronize + 0x166) [0x334a6]
=========     Host Frame:EigenTest (_Z4testv + 0x96) [0xd8b]
=========     Host Frame:EigenTest (main + 0x9) [0xcd9]
=========     Host Frame:/lib64/libc.so.6 (__libc_start_main + 0xfd) [0x1ed1d]
=========     Host Frame:EigenTest [0xc09]
=========

On my system I have Cuda 8.0.44 and Quadro M5000. My guess is that somewhere in the Eigen it's trying to call 'host' function. But I wasn't able to find it. Hopefully it should be easy to reproduce it, I was able to get my application freezing every single time. Also checked the available system/device memory prior to test. I had free 62GB system/8GB device memory.

Attached project for your reference.

Many Thanks
Comment 1 Ali Nakipoglu 2017-04-21 09:34:17 UTC
I managed to find a workaround:

EigenTranslationT translation( ... );
EigenQuaternionT rotation( ... );
EigenTransformT scale;

scale.linear().diagonal()   = EigenVectorT( .... );

EigenTransformT transform   = translation * rotation * scale; 

I don't understand why this is works but not Transform::fromPositionOrientationScale. The only difference I can see is how or which DiagonalMatrix methods called.
Comment 2 Nobody 2019-12-04 16:56:18 UTC
-- GitLab Migration Automatic Message --

This bug has been migrated to gitlab.com's GitLab instance and has been closed from further activity.

You can subscribe and participate further through the new bug through this link to our GitLab instance: https://gitlab.com/libeigen/eigen/issues/1415.

Note You need to log in before you can comment on or make changes to this bug.