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: 500,014
RAC: 1,136
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_geeProject donor
Volunteer developer
Volunteer tester
Avatar
Send message
Joined: 24 Nov 06
Posts: 4954
Credit: 72,903,894
RAC: 11,647
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