Skip to content

Commit cc96310

Browse files
author
roxx30198
committed
Updating reference docs
1 parent f562bd6 commit cc96310

File tree

18 files changed

+201
-189
lines changed

18 files changed

+201
-189
lines changed

‎docs/source/user_guide/debugging/debugging_environment.rst‎

Lines changed: 0 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -9,7 +9,6 @@ Configure debugging environment
99
1010
export ONEAPI_ROOT=/path/to/oneapi
1111
source $ONEAPI_ROOT/debugger/latest/env/vars.sh
12-
source $ONEAPI_ROOT/compiler/latest/env/vars.sh
1312
1413
2) Create and activate conda environment with the installed numba-dpex:
1514

‎numba_dpex/examples/debug/commands/docs/backtrace‎

Lines changed: 10 additions & 11 deletions
Original file line numberDiff line numberDiff line change
@@ -1,18 +1,17 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
3-
(gdb) break simple_dpex_func.py:22
3+
(gdb) break simple_dpex_func.py:12
44
(gdb) run simple_dpex_func.py
55
...
6-
Thread 2.2 hit Breakpoint 1, with SIMD lanes [0-7], __main__::func_sum () at simple_dpex_func.py:22
7-
22 result = a_in_func + b_in_func
6+
Thread 13 "python" hit Breakpoint 2, __main__::func_sum_242dpex_fn[abi:v2][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](float, float) (
7+
a_in_func=5, b_in_func=5) at simple_dpex_func.py:12
8+
12 result = a_in_func + b_in_func # breakpoint location
89
(gdb) backtrace
9-
#0 __main__::func_sum () at simple_dpex_func.py:22
10-
#1 __main__::kernel_sum () at simple_dpex_func.py:29
10+
#0 __main__::func_sum_242dpex_fn[abi:v2][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](float, float) (a_in_func=5, b_in_func=5)
11+
at simple_dpex_func.py:12
1112
(gdb) continue
1213
...
13-
[Switching to Thread 1.1073742080 lane 0]
14-
Thread 2.3 hit Breakpoint 1, with SIMD lanes [0-1], __main__::func_sum () at simple_dpex_func.py:22
15-
22 result = a_in_func + b_in_func
16-
(gdb) continue
14+
Thread 15 "python" hit Breakpoint 2, __main__::func_sum_242dpex_fn[abi:v2][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](float, float) (
15+
a_in_func=6, b_in_func=6) at simple_dpex_func.py:12
16+
12 result = a_in_func + b_in_func # breakpoint location
1717
...
18-
Done...

‎numba_dpex/examples/debug/commands/docs/backtrace_kernel‎

Lines changed: 8 additions & 12 deletions
Original file line numberDiff line numberDiff line change
@@ -1,17 +1,13 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
3-
(gdb) break simple_dpex_func.py:28
3+
(gdb) break simple_dpex_func.py:18
44
(gdb) run simple_dpex_func.py
55
...
6-
Thread 2.2 hit Breakpoint 1, with SIMD lanes [0-7], __main__::kernel_sum () at simple_dpex_func.py:28
7-
28 i = dpex.get_global_id(0)
6+
Thread 9 "python" hit Breakpoint 1, __main__::kernel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](DpnpNdArray<
7+
float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>) (a_in_kernel=..., b_in_kernel=...,
8+
c_in_kernel=...) at simple_dpex_func.py:18
9+
18 i = ndpx.get_global_id(0)
810
(gdb) backtrace
9-
#0 __main__::kernel_sum () at simple_dpex_func.py:28
10-
(gdb) continue
11+
#0 __main__::kernel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<
12+
float, 1, C, opencl_cpu>) (a_in_kernel=..., b_in_kernel=..., c_in_kernel=...) at simple_dpex_func.py:18
1113
...
12-
[Switching to Thread 1.1073742080 lane 0]
13-
Thread 2.3 hit Breakpoint 1, with SIMD lanes [0-1], __main__::kernel_sum () at simple_dpex_func.py:28
14-
28 i = dpex.get_global_id(0)
15-
(gdb) continue
16-
...
17-
Done...

‎numba_dpex/examples/debug/commands/docs/break_conditional‎

Lines changed: 5 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -1,12 +1,11 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
3-
(gdb) break simple_sum.py:23 if i == 1
3+
(gdb) break simple_sum.py:14 if i == 1
44
(gdb) run simple_sum.py
55
...
6-
Thread 2.2 hit Breakpoint 1, with SIMD lane 1, __main__::data_parallel_sum () at simple_sum.py:23
7-
23 c[i] = a[i] + b[i]
6+
Thread 11 "python" hit Breakpoint 1, __main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](DpnpNdArray<
7+
float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>) (a=..., b=..., c=...) at simple_sum.py:14
8+
14 c[i] = a[i] + b[i] # Condition breakpoint location
89
(gdb) print i
910
$1 = 1
10-
(gdb) continue
1111
...
12-
Done...

‎numba_dpex/examples/debug/commands/docs/break_file_func‎

Lines changed: 1 addition & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -1,4 +1,4 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
33
(gdb) break simple_sum.py:data_parallel_sum
44
(gdb) run simple_sum.py
@@ -8,6 +8,4 @@ Thread 2.2 hit Breakpoint 1, with SIMD lanes [0-7], __main__::data_parallel_sum
88
(gdb) continue
99
Thread 2.3 hit Breakpoint 1, with SIMD lanes [0-1], __main__::data_parallel_sum () at simple_sum.py:20
1010
20 @dpex.kernel(debug=True)
11-
(gdb) continue
1211
...
13-
Done...

‎numba_dpex/examples/debug/commands/docs/break_func‎

Lines changed: 2 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -1,4 +1,4 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
33
(gdb) break data_parallel_sum
44
(gdb) run simple_sum.py
@@ -8,6 +8,5 @@ Thread 2.2 hit Breakpoint 1, with SIMD lanes [0-7], __main__::data_parallel_sum
88
(gdb) continue
99
Thread 2.3 hit Breakpoint 1, with SIMD lanes [0-1], __main__::data_parallel_sum () at simple_sum.py:20
1010
20 @dpex.kernel(debug=True)
11-
(gdb) continue
11+
1212
...
13-
Done...

‎numba_dpex/examples/debug/commands/docs/break_line_number‎

Lines changed: 10 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -1,13 +1,15 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
3-
(gdb) break simple_sum.py:20
3+
(gdb) break simple_sum.py:11
44
(gdb) run simple_sum.py
55
...
6-
Thread 2.2 hit Breakpoint 1, with SIMD lanes [0-7], __main__::data_parallel_sum () at simple_sum.py:20
7-
20 @dpex.kernel(debug=True)
8-
(gdb) continue
9-
Thread 2.3 hit Breakpoint 1, with SIMD lanes [0-1], __main__::data_parallel_sum () at simple_sum.py:20
10-
20 @dpex.kernel(debug=True)
6+
Thread 12 "python" hit Breakpoint 1, __main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](DpnpNdArray<
7+
float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>) (a=..., b=..., c=...) at simple_sum.py:13
8+
13 i = ndpx.get_global_id(0)
119
(gdb) continue
10+
[Switching to thread 15 (Thread 0x7fff55cc0640 (LWP 44013))]
11+
12+
Thread 15 "python" hit Breakpoint 1, __main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](DpnpNdArray<
13+
float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>) (a=..., b=..., c=...) at simple_sum.py:13
14+
13 i = ndpx.get_global_id(0)
1215
...
13-
Done...

‎numba_dpex/examples/debug/commands/docs/break_nested_func‎

Lines changed: 2 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -1,4 +1,4 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
33
(gdb) break simple_dpex_func.py:func_sum
44
(gdb) run simple_dpex_func.py
@@ -8,6 +8,5 @@ Thread 2.2 hit Breakpoint 1, with SIMD lanes [0-7], __main__::func_sum () at sim
88
(gdb) continue
99
Thread 2.3 hit Breakpoint 1, with SIMD lanes [0-1], __main__::func_sum () at simple_dpex_func.py:22
1010
22 result = a_in_func + b_in_func
11-
(gdb) continue
11+
1212
...
13-
Done...

‎numba_dpex/examples/debug/commands/docs/info_func‎

Lines changed: 15 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -1,17 +1,26 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
3-
(gdb) break simple_sum.py:22
3+
(gdb) break simple_sum.py:12
44
(gdb) run simple_sum.py
55
(gdb) info functions data_parallel_sum
66
...
77
All functions matching regular expression "data_parallel_sum":
8+
89
File simple_sum.py:
9-
20: void __main__::data_parallel_sum(Array<float, 1, C, mutable, aligned>, Array<float, 1, C, mutable, aligned>, Array<float, 1, C, mutable, aligned>);
10+
12: i8 **__main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](DpnpNdArray<float, 1, C, opencl_cpu>,
11+
DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>);
1012
(gdb) continue
13+
[Switching to thread 12 (Thread 0x7fff564c2640 (LWP 44543))]
14+
15+
Thread 12 "python" hit Breakpoint 1, __main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](
16+
DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>) (a=..., b=..., c=...) at simple_sum.py:13
17+
13 i = ndpx.get_global_id(0)
1118
(gdb) info functions __main__
1219
...
1320
All functions matching regular expression "__main__":
14-
20: void __main__::data_parallel_sum(Array<float, 1, C, mutable, aligned>, Array<float, 1, C, mutable, aligned>, Array<float, 1, C, mutable, aligned>);
15-
(gdb) continue
21+
22+
File simple_sum.py:
23+
12: i8 **__main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](
24+
DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>);
25+
1626
...
17-
Done...

‎numba_dpex/examples/debug/commands/docs/local_variables_0‎

Lines changed: 37 additions & 58 deletions
Original file line numberDiff line numberDiff line change
@@ -1,81 +1,60 @@
1-
$ NUMBA_OPT=0 gdb-oneapi -q python
1+
$ NUMBA_OPT=0 NUMBA_DPEX_OPT=0 gdb-oneapi -q python
22
(gdb) set breakpoint pending on
3-
(gdb) break sum_local_vars.py:22
3+
(gdb) break sum_local_vars.py:13
44
(gdb) run sum_local_vars.py
55
...
6-
Thread 2.2 hit Breakpoint 1, with SIMD lanes [0-7], __main__::data_parallel_sum () at sum_local_vars.py:22
7-
22 i = dpex.get_global_id(0)
6+
Thread 11 "python" hit Breakpoint 1, __main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](
7+
DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>) (a=..., b=..., c=...)
8+
at sum_local_vars.py:13
9+
13 i = ndpx.get_global_id(0)
810
(gdb) info locals
9-
a = '\000' <repeats 55 times>
10-
b = '\000' <repeats 55 times>
11-
c = '\000' <repeats 55 times>
11+
__ocl_dbg_gid0 = 2
12+
__ocl_dbg_gid1 = 0
13+
__ocl_dbg_gid2 = 0
1214
i = 0
1315
l1 = 0
1416
l2 = 0
15-
__ocl_dbg_gid0 = 0
16-
__ocl_dbg_gid1 = 0
17-
__ocl_dbg_gid2 = 0
18-
__ocl_dbg_lid0 = 0
19-
__ocl_dbg_lid1 = 0
20-
__ocl_dbg_lid2 = 0
21-
__ocl_dbg_grid0 = 0
22-
__ocl_dbg_grid1 = 0
23-
__ocl_dbg_grid2 = 0
2417
(gdb) next
25-
Thread 2.3 hit Breakpoint 1, with SIMD lanes [0-1], __main__::data_parallel_sum () at sum_local_vars.py:22
26-
22 i = dpex.get_global_id(0)
18+
[Switching to thread 1 (Thread 0x7ffff7c71740 (LWP 45181))]
19+
20+
Thread 1 "python" hit Breakpoint 1, __main__::data_parallel_sum_241dpex_fn[abi:v1][abi:c8tJTC_2fWgMemLSg1AEMDLWKQhCFpAEkANV7BEpoA](
21+
DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>, DpnpNdArray<float, 1, C, opencl_cpu>) (a=..., b=..., c=...)
22+
at sum_local_vars.py:13
23+
13 i = ndpx.get_global_id(0)
2724
(gdb) next
2825
23 l1 = a[i] + 2.5
2926
(gdb) next
3027
24 l2 = b[i] * 0.3
3128
(gdb) info locals
32-
a = '\000' <repeats 55 times>
33-
b = '\000' <repeats 16 times>, "\n\000\000\000\000\000\000\000\004\000\000\000\000\000\000\000\000\240\016XUU\000\000\n\000\000\000\000\000\000\000\004\000\000\000\000\000\000"
34-
c = '\000' <repeats 16 times>, "\n\000\000\000\000\000\000\000\004\000\000\000\000\000\000\000\000@\256WUU\000\000\n\000\000\000\000\000\000\000\004\000\000\000\000\000\000"
35-
i = 8
36-
l1 = 2.5931931659579277
37-
l2 = 0
38-
__ocl_dbg_gid0 = 0
29+
__ocl_dbg_gid0 = 3
3930
__ocl_dbg_gid1 = 0
4031
__ocl_dbg_gid2 = 0
41-
__ocl_dbg_lid0 = 42949672970
42-
__ocl_dbg_lid1 = 0
43-
__ocl_dbg_lid2 = 93825037590528
44-
__ocl_dbg_grid0 = 4612811918334230528
45-
__ocl_dbg_grid1 = 0
46-
__ocl_dbg_grid2 = 0
47-
(gdb) next
48-
25 c[i] = l1 + l2
49-
(gdb) info locals
50-
a = '\000' <repeats 55 times>
51-
b = '\000' <repeats 55 times>
52-
c = '\000' <repeats 16 times>, "\n\000\000\000\000\000\000\000\004\000\000\000\000\000\000\000\000@\256WUU\000\000\n\000\000\000\000\000\000\000\004\000\000\000\000\000\000"
53-
i = 8
54-
l1 = 2.5931931659579277
55-
l2 = 0.22954882979393004
56-
__ocl_dbg_gid0 = 0
57-
__ocl_dbg_gid1 = 8
58-
__ocl_dbg_gid2 = 8
59-
__ocl_dbg_lid0 = 93825034429928
60-
__ocl_dbg_lid1 = 0
61-
__ocl_dbg_lid2 = 93825034429936
62-
__ocl_dbg_grid0 = 4599075939470750515
63-
__ocl_dbg_grid1 = 0
64-
__ocl_dbg_grid2 = 0
32+
i = 3
33+
l1 = 3.4331700205802917
34+
l2 = 0
6535
(gdb) print a
66-
$1 = '\000' <repeats 55 times>
36+
$1 = {meminfo = 0x0, parent = 0x0, nitems = 0, itemsize = 0, data = 0x0, sycl_queue = 0x0, shape = {0}, strides = {0}}
6737
(gdb) print l1
68-
$3 = 2.5931931659579277
38+
$2 = 2.5931931659579277
6939
(gdb) print l2
70-
$4 = 0.22954882979393004
40+
$4 = 0
7141
(gdb) ptype a
72-
type = byte [56]
42+
type = struct DpnpNdArray(dtype=float32, ndim=1, layout=C, address_space=1, usm_type=device, device=opencl:cpu:0, sycl_queue=DpctlSyclQueue on opencl:cpu:0)
43+
({float addrspace(1)*, i8* addrspace(1)*, i64, i64, float addrspace(1)*, i8* addrspace(1)*, [1 x i64], [1 x i64]}) {
44+
float *meminfo;
45+
i8 **parent;
46+
int64 nitems;
47+
int64 itemsize;
48+
float *data;
49+
i8 **sycl_queue;
50+
i64 shape[1];
51+
i64 strides[1];
52+
}
7353
(gdb) whatis a
74-
type = byte [56]
54+
type = DpnpNdArray(dtype=float32, ndim=1, layout=C, address_space=1, usm_type=device, device=opencl:cpu:0, sycl_queue=DpctlSyclQueue on opencl:cpu:0)
55+
({float addrspace(1)*, i8* addrspace(1)*, i64, i64, float addrspace(1)*, i8* addrspace(1)*, [1 x i64], [1 x i64]})
7556
(gdb) ptype l1
76-
type = double
57+
type = float64
7758
(gdb) whatis l1
78-
type = double
79-
(gdb) continue
59+
type = float64
8060
...
81-
Done...

0 commit comments

Comments
 (0)