BSOD 0x000000EA infinite loop nv4_disp


log in

Advanced search

Questions and Answers : GPU applications : BSOD 0x000000EA infinite loop nv4_disp

Author Message
akropol
Send message
Joined: 6 Jun 09
Posts: 1
Credit: 524,142
RAC: 45
Russia
Message 1449995 - Posted: 4 Dec 2013, 20:27:59 UTC

Hi all.
I get this error when I using GPU on my BOINC in a few second after beginning.
Config:
BOINC 7.2.33
OS Windows XP Professional x86 SP3
GPU NVIDIA GeForce 9600 GT (511MB) driver: 331.82 OpenCL: 1.00
CPU Intel Core2 Duo CPU E8400 @ 3.00GHz

I readed this thread: http://setiathome.berkeley.edu/forum_thread.php?id=55958 , but it's not contain solution.

I create cc_config.xml file in BOINC Data directory and disable screensaver, but BSODs still does.
Logs: stderrdae.txt is empty.
stdoutdae.txt

04-Dec-2013 01:57:10 [---] Starting BOINC client version 7.2.33 for windows_intelx86 04-Dec-2013 01:57:10 [---] log flags: file_xfer, sched_ops, task, coproc_debug 04-Dec-2013 01:57:10 [---] Libraries: libcurl/7.25.0 OpenSSL/1.0.1 zlib/1.2.6 04-Dec-2013 01:57:10 [---] Data directory: H:\Documents and Settings\All Users\Application Data\BOINC 04-Dec-2013 01:57:10 [---] Running under account Alex 04-Dec-2013 01:57:10 [---] [coproc] launching child process at H:\Program Files\BOINC\\boinc.exe 04-Dec-2013 01:57:10 [---] [coproc] relative to directory H:\Documents and Settings\All Users\Application Data\BOINC 04-Dec-2013 01:57:10 [---] [coproc] with data directory "H:\Documents and Settings\All Users\Application Data\BOINC" 04-Dec-2013 01:57:10 [---] CUDA: NVIDIA GPU 0: GeForce 9600 GT (driver version 331.82, CUDA version 6.0, compute capability 1.1, 512MB, 477MB available, 336 GFLOPS peak) 04-Dec-2013 01:57:10 [---] OpenCL: NVIDIA GPU 0: GeForce 9600 GT (driver version 331.82, device version OpenCL 1.0 CUDA, 512MB, 477MB available, 336 GFLOPS peak) 04-Dec-2013 01:57:10 [---] NVIDIA library reports 1 GPU 04-Dec-2013 01:57:10 [---] No usable CAL devices found 04-Dec-2013 01:57:10 [---] Host name: home-f311a9eff0 04-Dec-2013 01:57:10 [---] Processor: 2 GenuineIntel Intel(R) Core(TM)2 Duo CPU E8400 @ 3.00GHz [Family 6 Model 23 Stepping 10] 04-Dec-2013 01:57:10 [---] Processor features: fpu vme de pse tsc msr pae mce cx8 apic sep mtrr pge mca cmov pat pse36 clflush dts acpi mmx fxsr sse sse2 ss htt tm pni ssse3 cx16 sse4_1 nx lm vmx smx tm2 pbe 04-Dec-2013 01:57:10 [---] OS: Microsoft Windows XP: Professional x86 Edition, Service Pack 3, (05.01.2600.00) 04-Dec-2013 01:57:10 [---] Memory: 3.25 GB physical, 5.11 GB virtual 04-Dec-2013 01:57:10 [---] Disk: 25.48 GB total, 1.59 GB free 04-Dec-2013 01:57:10 [---] Local time is UTC +4 hours 04-Dec-2013 01:57:10 [SETI@home] URL http://setiathome.berkeley.edu/; Computer ID 4974951; resource share 100 04-Dec-2013 01:57:10 [SETI@home] General prefs: from SETI@home (last modified 03-Dec-2013 19:44:20) 04-Dec-2013 01:57:10 [SETI@home] Host location: none 04-Dec-2013 01:57:10 [SETI@home] General prefs: using your defaults 04-Dec-2013 01:57:10 [---] Reading preferences override file 04-Dec-2013 01:57:10 [---] Preferences: 04-Dec-2013 01:57:10 [---] max memory usage when active: 1663.49MB 04-Dec-2013 01:57:10 [---] max memory usage when idle: 2994.28MB 04-Dec-2013 01:57:10 [---] max disk usage: 0.60GB 04-Dec-2013 01:57:10 [---] suspend work if non-BOINC CPU load exceeds 75% 04-Dec-2013 01:57:10 [---] (to change preferences, visit a project web site or select Preferences in the Manager) 04-Dec-2013 01:57:10 [---] Not using a proxy 04-Dec-2013 01:57:11 Initialization completed 04-Dec-2013 01:57:11 [SETI@home] Restarting task 28mr08ah.23645.890.13.12.247_0 using setiathome_v7 version 700 in slot 0 04-Dec-2013 01:57:11 [SETI@home] Restarting task 04mr08af.19980.2935.11.12.251_0 using setiathome_v7 version 700 in slot 1 04-Dec-2013 01:57:16 [SETI@home] work fetch resumed by user ==== SKIP - calculating CPU tasks ==== 04-Dec-2013 21:52:37 [---] Resuming GPU computation 04-Dec-2013 21:52:41 [SETI@home] General prefs: from SETI@home (last modified 03-Dec-2013 19:44:20) 04-Dec-2013 21:52:41 [SETI@home] Host location: none 04-Dec-2013 21:52:41 [SETI@home] General prefs: using your defaults 04-Dec-2013 21:52:41 [---] Reading preferences override file 04-Dec-2013 21:52:41 [---] Preferences: 04-Dec-2013 21:52:41 [---] max memory usage when active: 1663.49MB 04-Dec-2013 21:52:41 [---] max memory usage when idle: 2994.28MB 04-Dec-2013 21:52:41 [---] max disk usage: 0.54GB 04-Dec-2013 21:52:41 [---] suspend work if non-BOINC CPU load exceeds 75% 04-Dec-2013 21:52:41 [---] (to change preferences, visit a project web site or select Preferences in the Manager) 04-Dec-2013 21:52:45 [SETI@home] work fetch resumed by user 04-Dec-2013 21:52:47 [SETI@home] Sending scheduler request: To fetch work. 04-Dec-2013 21:52:47 [SETI@home] Requesting new tasks for CPU and NVIDIA 04-Dec-2013 21:52:51 [SETI@home] Scheduler request completed: got 17 new tasks 04-Dec-2013 21:52:53 [SETI@home] Started download of setiathome_7.00_windows_intelx86__cuda32.exe 04-Dec-2013 21:52:53 [SETI@home] Started download of cudart32_32_16.dll 04-Dec-2013 21:52:58 [SETI@home] Finished download of cudart32_32_16.dll 04-Dec-2013 21:52:58 [SETI@home] Started download of cufft32_32_16.dll 04-Dec-2013 21:53:06 [SETI@home] work fetch suspended by user 04-Dec-2013 21:53:07 [SETI@home] Finished download of setiathome_7.00_windows_intelx86__cuda32.exe 04-Dec-2013 21:53:07 [SETI@home] Started download of mbcuda-7.00-cuda32.cfg.sample 04-Dec-2013 21:53:08 [SETI@home] Finished download of mbcuda-7.00-cuda32.cfg.sample 04-Dec-2013 21:53:08 [SETI@home] Started download of mbcuda-7.00-cuda32.cfg 04-Dec-2013 21:53:09 [SETI@home] Finished download of mbcuda-7.00-cuda32.cfg 04-Dec-2013 21:53:09 [SETI@home] Started download of setiathome-7.00-cuda32_AUTHORS.txt 04-Dec-2013 21:53:10 [SETI@home] Finished download of setiathome-7.00-cuda32_AUTHORS.txt 04-Dec-2013 21:53:10 [SETI@home] Started download of setiathome-7.00-cuda32_COPYING.txt 04-Dec-2013 21:53:14 [SETI@home] Finished download of setiathome-7.00-cuda32_COPYING.txt 04-Dec-2013 21:53:14 [SETI@home] Started download of setiathome-7.00-cuda32_COPYRIGHT.txt 04-Dec-2013 21:53:15 [SETI@home] Finished download of setiathome-7.00-cuda32_COPYRIGHT.txt 04-Dec-2013 21:53:15 [SETI@home] Started download of setiathome-7.00-cuda32_README.txt 04-Dec-2013 21:53:17 [SETI@home] Finished download of setiathome-7.00-cuda32_README.txt 04-Dec-2013 21:53:17 [SETI@home] Started download of setiathome-7.00-cuda32_README_x41zc.txt 04-Dec-2013 21:53:20 [SETI@home] Finished download of setiathome-7.00-cuda32_README_x41zc.txt 04-Dec-2013 21:53:20 [SETI@home] Started download of 14au08ae.6063.296560.6.12.30 04-Dec-2013 21:53:25 [SETI@home] Finished download of cufft32_32_16.dll 04-Dec-2013 21:53:25 [SETI@home] Started download of 14au08ae.6063.296560.6.12.96 04-Dec-2013 21:53:28 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.30 04-Dec-2013 21:53:28 [SETI@home] Started download of 20ja09af.11763.10707.3.12.71 04-Dec-2013 21:53:28 [SETI@home] [coproc] Assigning NVIDIA instance 0 to 14au08ae.6063.296560.6.12.30_1 04-Dec-2013 21:53:28 [SETI@home] Starting task 14au08ae.6063.296560.6.12.30_1 using setiathome_v7 version 700 (cuda32) in slot 2 04-Dec-2013 21:53:32 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.96 04-Dec-2013 21:53:32 [SETI@home] Finished download of 20ja09af.11763.10707.3.12.71 04-Dec-2013 21:53:32 [SETI@home] Started download of 14au08ae.6063.296560.6.12.102 04-Dec-2013 21:53:32 [SETI@home] Started download of 14au08ae.6063.296560.6.12.28 04-Dec-2013 21:53:32 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.30_1 04-Dec-2013 21:53:37 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.102 04-Dec-2013 21:53:37 [SETI@home] Started download of 14au08ae.6063.296560.6.12.192 04-Dec-2013 21:53:37 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.30_1 04-Dec-2013 21:53:43 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.28 04-Dec-2013 21:53:43 [SETI@home] Started download of 20ja09af.11763.10707.3.12.91 04-Dec-2013 21:53:43 [SETI@home] [coproc] Assigning NVIDIA instance 0 to 20ja09af.11763.10707.3.12.71_1 04-Dec-2013 21:53:43 [SETI@home] Starting task 20ja09af.11763.10707.3.12.71_1 using setiathome_v7 version 700 (cuda32) in slot 3 04-Dec-2013 21:53:48 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.192 04-Dec-2013 21:53:48 [SETI@home] Started download of 14au08ae.6063.296560.6.12.108 04-Dec-2013 21:53:48 [SETI@home] [coproc] NVIDIA instance 0: confirming for 20ja09af.11763.10707.3.12.71_1 04-Dec-2013 21:53:52 [SETI@home] Finished download of 20ja09af.11763.10707.3.12.91 04-Dec-2013 21:53:52 [SETI@home] Started download of 14au08ae.6063.296560.6.12.200 04-Dec-2013 21:53:52 [SETI@home] [coproc] NVIDIA instance 0: confirming for 20ja09af.11763.10707.3.12.71_1 04-Dec-2013 21:53:55 [SETI@home] [coproc] Assigning NVIDIA instance 0 to 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:53:55 [SETI@home] Starting task 14au08ae.6063.296560.6.12.192_1 using setiathome_v7 version 700 (cuda32) in slot 4 04-Dec-2013 21:53:57 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.108 04-Dec-2013 21:53:57 [SETI@home] Started download of 14au08ae.6063.296560.6.12.114 04-Dec-2013 21:53:57 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:53:59 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.200 04-Dec-2013 21:53:59 [SETI@home] Started download of 14au08ae.6063.296560.6.12.204 04-Dec-2013 21:53:59 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:54:06 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.204 04-Dec-2013 21:54:06 [SETI@home] Started download of 14au08ae.6063.296560.6.12.120 04-Dec-2013 21:54:06 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:54:12 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.114 04-Dec-2013 21:54:12 [SETI@home] Started download of 20ja09af.11763.10707.3.12.75 04-Dec-2013 21:54:12 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:54:15 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.120 04-Dec-2013 21:54:15 [SETI@home] Started download of 20ja09af.11763.10707.3.12.62 04-Dec-2013 21:54:15 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:54:16 [SETI@home] Finished download of 20ja09af.11763.10707.3.12.75 04-Dec-2013 21:54:16 [SETI@home] Started download of 20ja09af.11763.10707.3.12.120 04-Dec-2013 21:54:16 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:54:18 [SETI@home] Finished download of 20ja09af.11763.10707.3.12.62 04-Dec-2013 21:54:18 [SETI@home] Finished download of 20ja09af.11763.10707.3.12.120 04-Dec-2013 21:54:18 [SETI@home] Started download of 14au08ae.6063.296560.6.12.181 04-Dec-2013 21:54:18 [SETI@home] Started download of 20ja09af.11763.10707.3.12.50 04-Dec-2013 21:54:18 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:54:21 [SETI@home] Finished download of 14au08ae.6063.296560.6.12.181 04-Dec-2013 21:54:21 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1 04-Dec-2013 21:54:23 [SETI@home] Finished download of 20ja09af.11763.10707.3.12.50 04-Dec-2013 21:54:23 [SETI@home] [coproc] NVIDIA instance 0: confirming for 14au08ae.6063.296560.6.12.192_1


./slots/2/stderr.txt
setiathome_CUDA: Found 1 CUDA device(s):
Device 1: GeForce 9600 GT, 511 MiB, regsPerBlock 8192
computeCap 1.1, multiProcs 8
pciBusID = 1, pciSlotID = 0
clockRate = 1750 MHz
In cudaAcc_initializeDevice(): Boinc passed DevPref 1
setiathome_CUDA: CUDA Device 1 specified, checking...
Device 1: GeForce 9600 GT is okay
SETI@home using CUDA accelerated device GeForce 9600 GT
pulsefind: blocks per SM 1 (Pre-Fermi default)
pulsefind: periods per launch 100 (default)
Priority of process set to BELOW_NORMAL (default) successfully
Priority of worker thread set successfully

setiathome enhanced x41zc, Cuda 3.20

Detected setiathome_enhanced_v7 task. Autocorrelations enabled, size 128k elements.
Work Unit Info:
...............
WU true angle range is : 1.532882
re-using dev_GaussFitResults array for dev_AutoCorrIn, 4194304 bytes
re-using dev_GaussFitResults+524288x8 array for dev_AutoCorrOut, 4194304 bytes
Error on call (cudaMemcpy(PowerSpectrumSumMax, dev_PowerSpectrumSumMax, (cudaAcc_NumDataPoints / fftlen) * sizeof(*dev_PowerSpectrumSumMax), cudaMemcpyDeviceToHost)), file c:/[Projects]/__Sources/sah_v7_opt/Xbranch/client/cuda/cudaAcc_summax.cu, line 252: unspecified driver error
Exiting
cudaAcc_free() called...
cudaAcc_free() running...
cudaAcc_free() PulseFind freed...
cudaAcc_free() Gaussfit freed...
cudaAcc_free() AutoCorrelation freed...
cudaAcc_free() DONE.
Cuda sync'd & freed.
Preemptively acknowledging a safe temporary exit->
Exit Status: 0
boinc_exit(): requesting safe worker shutdown ->
boinc_exit(): received safe worker shutdown acknowledge ->
Cuda threadsafe ExitProcess() initiated, rval 0


./slots/2/stderr.txt


setiathome_CUDA: Found 1 CUDA device(s):
Device 1: GeForce 9600 GT, 511 MiB, regsPerBlock 8192
computeCap 1.1, multiProcs 8
pciBusID = 1, pciSlotID = 0
clockRate = 1750 MHz
In cudaAcc_initializeDevice(): Boinc passed DevPref 1
setiathome_CUDA: CUDA Device 1 specified, checking...
Device 1: GeForce 9600 GT is okay
SETI@home using CUDA accelerated device GeForce 9600 GT
pulsefind: blocks per SM 1 (Pre-Fermi default)
pulsefind: periods per launch 100 (default)
Priority of process set to BELOW_NORMAL (default) successfully
Priority of worker thread set successfully

setiathome enhanced x41zc, Cuda 3.20

Detected setiathome_enhanced_v7 task. Autocorrelations enabled, size 128k elements.
Work Unit Info:
...............
WU true angle range is : 6.853211
re-using dev_GaussFitResults array for dev_AutoCorrIn, 4194304 bytes
re-using dev_GaussFitResults+524288x8 array for dev_AutoCorrOut, 4194304 bytes
uncaptured error before call (cudaMemcpy(best_PoT, dev_tmp_pot, max_nb_of_elems * sizeof(float), cudaMemcpyDeviceToHost)), file c:/[Projects]/__Sources/sah_v7_opt/Xbranch/client/cuda/cudaAcc_pulsefind.cu, line 1622: unspecified driver error
Exiting
cudaAcc_free() called...
cudaAcc_free() running...
cudaAcc_free() PulseFind freed...
cudaAcc_free() Gaussfit freed...
cudaAcc_free() AutoCorrelation freed...
cudaAcc_free() DONE.
Cuda sync'd & freed.
Preemptively acknowledging a safe temporary exit->
Exit Status: 0
boinc_exit(): requesting safe worker shutdown ->
boinc_exit(): received safe worker shutdown acknowledge ->
Cuda threadsafe ExitProcess() initiated, rval 0

Profile jason_gee
Volunteer developer
Volunteer tester
Avatar
Send message
Joined: 24 Nov 06
Posts: 5087
Credit: 74,251,666
RAC: 6,393
Australia
Message 1450226 - Posted: 5 Dec 2013, 9:55:56 UTC
Last modified: 5 Dec 2013, 10:15:27 UTC

Hi, Something very weird going on, likely at low level.

I'd recommend start eliminating easy possibilities, starting with at least 2 loops of memtest86+, followed by ordinary disk checks, reseat the card and do some artefact scans. --> check temperatures etc, clean install driver. Easy things first.
____________
"It is not the strongest of the species that survives, nor the most intelligent that survives. It is the one that is the most adaptable to change."
Charles Darwin

Questions and Answers : GPU applications : BSOD 0x000000EA infinite loop nv4_disp

Copyright © 2014 University of California