Page MenuHomePhabricator
Create Paste
Paste All Pastes

All Pastes
Use Results
Edit Query

  • P115 clover address warnings
    ```
    ../../../src/mesa/src/gallium/state_trackers/clover/api/memory.cpp:228:53: warning: suggest braces around initialization of subobject [-Wmissing-braces]
    row_pitch, 0, 0, 0, NULL };
    ^~~~
    { }
    ...
    • Sep 24 2019, 7:04 PM
    • 75 Lines
    Author: pmoreau
  • P113 [MCP79][4.15] Kernel error
    -- Logs begin at Sat 2015-06-06 14:52:01 CEST, end at Thu 2018-01-18 00:25:56 CET. --
    Jan 18 00:19:17 archlinux kernel: Linux version 4.14.0-rc7-nouveau+ (pmoreau@Normandy) (gcc version 7.2.1 20171224 (GCC)) #3 SMP PREEMPT Wed Jan 17 23:56:26 CET 2018
    Jan 18 00:19:17 archlinux kernel: Command line: initrd=\10c24563ac9e431a983ea6b33bb38f27\4.14.0-rc7-nouveau+\initrd root=UUID="cd1828b1-4f94-42dc-bebe-c8d9a7767645" resume=UUID="1c09e7aa-268e-4a94-82a4-3ab024af8649" rootflags=subvol=@ rw quiet
    Jan 18 00:19:17 archlinux kernel: x86/fpu: Supporting XSAVE feature 0x001: 'x87 floating point registers'
    Jan 18 00:19:17 archlinux kernel: x86/fpu: Supporting XSAVE feature 0x002: 'SSE registers'
    ...
    • Jan 18 2018, 12:32 AM
    • 1,217 Lines
    Author: pmoreau
  • P112 Fix neg modifier on src1 for IADD on GM107+
    diff --git a/src/gallium/drivers/nouveau/codegen/nv50_ir_emit_gm107.cpp b/src/gallium/drivers/nouveau/codegen/nv50_ir_emit_gm107.cpp
    index b1e9f941fe..27f2dacca7 100644
    --- a/src/gallium/drivers/nouveau/codegen/nv50_ir_emit_gm107.cpp
    +++ b/src/gallium/drivers/nouveau/codegen/nv50_ir_emit_gm107.cpp
    @@ -1731,6 +1731,8 @@ CodeEmitterGM107::emitNOT()
    ...
    • Sep 26 2017, 1:20 AM
    • 37 Lines
    • Diff
    Author: pmoreau
  • P111 Old patch for clCreateProgramWithSource() support
    commit b14a3239296de45f72adc497141a1ff5fb2400e3
    Author: Pierre Moreau <pierre.morrow@free.fr>
    Date: Sat Apr 23 22:15:02 2016 +0200
    [HACK] clover: `clCreateProgramWithSource` using SPIR-V
    ...
    • Sep 20 2017, 1:26 AM
    • 476 Lines
    • Diff
    Author: pmoreau
  • P110 Display notification for e-mail
    #!/bin/python
    import gi
    import email
    import re
    ...
    • Sep 8 2017, 7:05 PM
    • 42 Lines
    • Python
    Author: pmoreau
  • P108 G80 errors while rotating screen
    -- Logs begin at Mon 2016-03-21 19:32:28 CET, end at Fri 2016-11-18 00:22:42 CET. --
    Nov 18 00:18:25 Rannoch systemd-journald[2353]: Time spent on flushing to /var is 680us for 0 entries.
    Nov 18 00:18:25 Rannoch kernel: Linux version 4.9.0-rc4-nouveau-73361-gb27add1 (pmoreau@Rannoch) (gcc version 6.2.1 20160830 (GCC) ) #6 SMP Sun Nov 13 13:35:36 CET 2016
    Nov 18 00:18:25 Rannoch kernel: Command line: initrd=\39d10a29e45849ff93dd2d023fbd8f8b\4.9.0-rc4-nouveau-73361-gb27add1\initrd root="UUID=d4930a96-2ae1-4275-8dd9-d8f3a979c2ae" rw init=/usr/lib/systemd/systemd quiet iomem=relaxed log_buf_len=8M nouveau.debug=disp=trace,i2c=trace drm.debug=0x14
    Nov 18 00:18:25 Rannoch kernel: x86/fpu: Supporting XSAVE feature 0x001: 'x87 floating point registers'
    ...
    • Nov 18 2016, 12:36 AM
    • 37,722 Lines
    Author: pmoreau
  • P107 GM206 MP counters
    Rannoch% GALLIUM_HUD="warps_launched" glxgears
    Running synchronized to the vertical refresh. The framerate should be
    approximately the same as the monitor refresh rate.
    ======== MP[0] =========
    ======== MP[1] =========
    ...
    • Nov 3 2016, 10:24 PM
    • 58 Lines
    Author: pmoreau
  • P106 CUDA project kernels (SM 5.2)
    Fatbin elf code:
    ================
    arch = sm_52
    code version = [1,7]
    ...
    • Oct 18 2016, 11:32 AM
    • 8,812 Lines
    Author: pmoreau
  • P105 SPIR-V -> NV50 IR: Texture R/W
    There are 1 platforms.
    There are 1 GPU devices.
    clCreateContext() succeeded.
    clCreateCommandQueue() succeeded.
    clCreateProgramWithIL() suceeded.
    ...
    • Sep 22 2016, 1:19 PM
    • 266 Lines
    Author: pmoreau
  • P104 SPIR-V Loop less-than
    % NV50_PROG_DEBUG=255 ../mesa_build/src/gallium/drivers/nouveau/nouveau_compiler -a e7 ./loop_lt.spv
    Compiling for NVE7
    translating program of type 5
    Parsing SPIR-V generated by 6 (version 14)
    Version 1.0
    ...
    • Sep 10 2016, 8:34 PM
    • 1,931 Lines
    Author: pmoreau
  • P103 GM20X Patch
    diff --git a/src/gallium/drivers/nouveau/nvc0/nvc0_context.h b/src/gallium/drivers/nouveau/nvc0/nvc0_context.h
    index 436e912..b5da41d 100644
    --- a/src/gallium/drivers/nouveau/nvc0/nvc0_context.h
    +++ b/src/gallium/drivers/nouveau/nvc0/nvc0_context.h
    @@ -298,6 +298,7 @@ void nvc0_fragprog_validate(struct nvc0_context *);
    ...
    • Aug 27 2016, 11:45 PM
    • 107 Lines
    • Diff
    Author: pmoreau
  • P102 nv_cmp_volt
    current voltage (µV), expected voltage (µV), abs diff (µV),rel diff nouveau/nvidia (%), pstate, cstate, temperature(°C)
    1025000, 1025000, 0, 100.000000, 15, 37, 70
    1025000, 1025000, 0, 100.000000, 15, 37, 69
    1025000, 1025000, 0, 100.000000, 15, 37, 70
    1025000, 1025000, 0, 100.000000, 15, 37, 69
    ...
    • Aug 21 2016, 11:53 PM
    • 428 Lines
    Author: pmoreau
  • P101 nouveau_backlight_v3.diff
    diff --git a/drm/Makefile b/drm/Makefile
    index 6d38d3a..466a987 100644
    --- a/drm/Makefile
    +++ b/drm/Makefile
    @@ -11,8 +11,8 @@ endif
    ...
    • Aug 5 2016, 8:09 PM
    • 184 Lines
    Author: pmoreau
  • P100 main.cu
    #include "config.hpp"
    #include "cuda.hpp"
    #include "opengl.hpp"
    #include "various.hpp"
    ...
    • Aug 2 2016, 4:01 PM
    • 244 Lines
    Author: pmoreau
  • P99 dnsmasq config
    port=0
    interface=ens9
    bind-interfaces
    dhcp-range=192.168.0.50,192.168.0.150,12h
    dhcp-boot=/arch/boot/syslinux/lpxelinux.0
    ...
    • Jul 26 2016, 11:17 PM
    • 10 Lines
    Author: pmoreau
  • P98 Split 64-bit MAD/MUL
    Instruction *
    BuildUtil::split64Mul(Function *fn, Instruction *i, Value *zero,
    Value *carry)
    {
    DataType hTy;
    ...
    • May 28 2016, 8:34 PM
    • 103 Lines
    • C++
    Author: pmoreau
  • P97 [GK107] Insns wrongly marked as useless
    % NV50_PROG_DEBUG=255 ../mesa_build/src/gallium/drivers/nouveau/nouveau_compiler -a e4 cast.spv 0 jobs
    Compiling for NVE4
    translating program of type 5
    Parsing SPIR-V generated by 6 (version 13)
    Version 1.0
    ...
    • May 14 2016, 11:57 PM
    • 235 Lines
    Author: pmoreau
  • P96 math: Import isinf and others to global namespace
    commit d7469ccc44763d0eeec4ee5c7c48c835df65a10e
    Author: Pierre Moreau <pierre.morrow@free.fr>
    Date: Wed Apr 13 23:35:50 2016 +0200
    math: Import isinf and others to global namespace
    ...
    • Apr 13 2016, 11:45 PM
    • 43 Lines
    Author: pmoreau
  • P95 [GK106] Wrong CVT from U64 to U32, as src became U32
    clCreateProgramWithSource() suceeded.
    clBuildProgram() suceeded.
    clCreateKernel() suceeded.
    clSetKernelArg() succeeded.
    translating program of type 5
    ...
    • Mar 6 2016, 3:35 AM
    • 422 Lines
    Author: pmoreau
  • P94 [GK106] Unknown opcode in CVT from U32 to U64
    ./get-global-id: /root/pmoreau/llvm_spirv/mesa_install/lib/libOpenCL.so.1: no version information available (required by ./get-global-id)
    There are 1 platforms.
    There are 1 GPU devices.
    TESS_CTRL
    PROPERTY TCS_VERTICES_OUT 1
    ...
    • Mar 6 2016, 1:54 AM
    • 112 Lines
    Author: pmoreau
  • P93 [GF119] hello_world
    Compiling for NVD9
    translating program of type 5
    Parsing SPIR-V generated by 7 (version 0)
    Version 1.0
    ID bound: 13
    ...
    • Mar 4 2016, 1:43 PM
    • 293 Lines
    Author: pmoreau
  • P92 [GM200] strace X
    execve("/usr/bin/X", ["X"], [/* 29 vars */]) = 0
    brk(NULL) = 0x1265000
    access("/etc/ld.so.preload", R_OK) = -1 ENOENT (No such file or directory)
    open("/home/pmoreau/userspaces/graphics/lib/tls/x86_64/libreadline.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (No such file or directory)
    stat("/home/pmoreau/userspaces/graphics/lib/tls/x86_64", 0x7ffc0ea22e90) = -1 ENOENT (No such file or directory)
    ...
    • Mar 2 2016, 3:17 PM
    • 589 Lines
    Author: pmoreau
  • P91 [GM200] Xorg.log.0
    [ 121.775]
    X.Org X Server 1.18.1
    Release Date: 2016-02-08
    [ 121.777] X Protocol Version 11, Revision 0
    [ 121.777] Build Operating System: Linux 4.2.5-1-ARCH x86_64
    ...
    • Mar 2 2016, 3:16 PM
    • 346 Lines
    Author: pmoreau
  • P90 `glxinfo -l -s` for 11.2-rc1
    name of display: :0
    display: :0 screen: 0
    direct rendering: Yes
    server glx vendor string: SGI
    server glx version string: 1.4
    ...
    • Feb 25 2016, 12:55 AM
    • 1,510 Lines
    Author: pmoreau
  • P89 [GM200][Nouveau] dmesg with 2560x1440 over DP + 1920x1200 over DVI-I
    [ 0.000000] Linux version 4.5.0-rc3-ARCH-174658-gd2eaa59 (pmoreau@Sovereign) (gcc version 5.3.0 (GCC) ) #2 SMP PREEMPT Mon Feb 22 11:25:50 CET 2016
    [ 0.000000] Command line: initrd=\48c211fd73ab4315a5fc69a5df61dc11\4.5.0-rc3-ARCH-174658-gd2eaa59\initrd root="UUID=3bcf4b8c-0fa5-4cfe-a048-1d3ef44c5c5c" rootflags=subvol=root rw init=/usr/lib/systemd/systemd quiet
    [ 0.000000] x86/fpu: xstate_offset[2]: 576, xstate_sizes[2]: 256
    [ 0.000000] x86/fpu: Supporting XSAVE feature 0x01: 'x87 floating point registers'
    [ 0.000000] x86/fpu: Supporting XSAVE feature 0x02: 'SSE registers'
    ...
    • Feb 23 2016, 1:29 PM
    • 1,001 Lines
    Author: pmoreau
  • P88 [GM200][Nouveau] dmesg
    [ 0.000000] Linux version 4.5.0-rc3-ARCH-174658-gd2eaa59 (pmoreau@Sovereign) (gcc version 5.3.0 (GCC) ) #2 SMP PREEMPT Mon Feb 22 11:25:50 CET 2016
    [ 0.000000] Command line: initrd=\48c211fd73ab4315a5fc69a5df61dc11\4.5.0-rc3-ARCH-174658-gd2eaa59\initrd root="UUID=3bcf4b8c-0fa5-4cfe-a048-1d3ef44c5c5c" rootflags=subvol=root rw init=/usr/lib/systemd/systemd systemd.unit=multi-user.target nouveau.debug=debug
    [ 0.000000] x86/fpu: xstate_offset[2]: 576, xstate_sizes[2]: 256
    [ 0.000000] x86/fpu: Supporting XSAVE feature 0x01: 'x87 floating point registers'
    [ 0.000000] x86/fpu: Supporting XSAVE feature 0x02: 'SSE registers'
    ...
    • Feb 23 2016, 1:28 PM
    • 3,268 Lines
    Author: pmoreau
  • P87 Load const vector
    ; SPIR-V
    ; Version: 1.0
    ; Generator: Khronos LLVM/SPIR-V Translator; 10
    ; Bound: 30
    ; Schema: 0
    ...
    • Feb 6 2016, 7:17 PM
    • 56 Lines
    Author: pmoreau
  • P86 Kepler: hello_world
    pi:6 ()
    BB:0 (2 instructions) - df = { }
    -> BB:2 (tree)
    0: ld u64 %r0d c0[0x0] (0)
    1: bra BB:2 (0)
    ...
    • Feb 1 2016, 11:11 PM
    • 44 Lines
    Author: pmoreau
  • P85 Aphront error when fetching public repo over https ro
    Feb 01 21:04:43 naccopic nginx[32639]: 2016/02/01 21:04:43 [error] 32653#0: *85 FastCGI sent in stderr: "PHP message: [2016-02-01 21:04:43] EXCEPTION: (AphrontQueryException) #1366: Incorrect integer value: '' for column 'remoteAddress' at row 1 at [<phutil>/src/aphront/storage/connection/mysql/AphrontBaseMySQLDatabaseConnection.php:340]
    Feb 01 21:04:43 naccopic nginx[32639]: PHP message: arcanist(head=master, ref.master=57f6fb59d739), phabricator(head=master, ref.master=d41aaba2a184), phutil(head=master, ref.master=f43291e99d36)
    Feb 01 21:04:43 naccopic nginx[32639]: PHP message: #0 <#2> AphrontBaseMySQLDatabaseConnection::throwQueryCodeException(integer, string) called at [<phutil>/src/aphront/storage/connection/mysql/AphrontBaseMySQLDatabaseConnection.php:275]
    Feb 01 21:04:43 naccopic nginx[32639]: PHP message: #1 <#2> AphrontBaseMySQLDatabaseConnection::throwQueryException(mysqli) called at [<phutil>/src/aphront/storage/connection/mysql/AphrontBaseMySQLDatabaseConnection.php:181]
    Feb 01 21:04:43 naccopic nginx[32639]: PHP message: #2 <#2> AphrontBaseMySQLDatabaseConnection::executeRawQuery(string) called at [<phutil>/src/xsprintf/queryfx.php:6]
    ...
    • Feb 1 2016, 9:06 PM
    • 12 Lines
    Author: pmoreau
  • P84 SchedDataCalculator crashes for hello_world on Kepler+
    clCreateCommandQueue() succeeded.
    clCreateProgramWithSource() suceeded.
    clBuildProgram() suceeded.
    clCreateKernel() suceeded.
    clCreateBuffer() succeeded.
    ...
    • Jan 28 2016, 9:39 PM
    • 240 Lines
    Author: pmoreau
  • P83 phabricator script
    #!/bin/zsh
    #
    # $1: action "stop", "start", "restart"
    ...
    • Jan 28 2016, 8:38 PM
    • 34 Lines
    Author: pmoreau
  • P82 phabricator.target
    [Unit]
    Description=Phabricator
    After=network.service multi-user.target
    [Install]
    ...
    • Jan 28 2016, 8:37 PM
    • 6 Lines
    Author: pmoreau
  • P81 phabricator-sshd.service
    [Unit]
    Description=Phabricator OpenSSH Daemon
    Wants=sshdgenkeys.service
    After=sshdgenkeys.service
    After=network.target
    ...
    • Jan 28 2016, 8:36 PM
    • 14 Lines
    Author: pmoreau
  • P80 phabricator-phd.service
    [Unit]
    Description=Phabricator daemon controller
    After=network.target
    [Service]
    ...
    • Jan 28 2016, 8:36 PM
    • 14 Lines
    Author: pmoreau
  • P79 phabricator-aphlict.service
    [Unit]
    Description=Phabricator notification service
    After=network.target
    [Service]
    ...
    • Jan 28 2016, 8:35 PM
    • 14 Lines
    Author: pmoreau
  • P78 SPIR-V vec-load fails on Tesla
    ./vec-load: /home/pmoreau/userspaces/llvm_spirv/lib/libOpenCL.so.1: no version information available (required by ./vec-load)
    There are 1 platforms.
    There are 1 GPU devices.
    clCreateProgramWithSource() suceeded.
    clBuildProgram() suceeded.
    ...
    • Jan 26 2016, 10:12 PM
    • 547 Lines
    Author: pmoreau
  • P77 SPIR-V FunctionCall Fail
    % NV50_PROG_DEBUG=255 nouveau_compiler -a 96 function_call.spv 1 jobs
    Compiling for NV96
    translating program of type 5
    Parsing SPIR-V generated by 6 (version 10)
    Version 1.0
    ...
    • Jan 24 2016, 10:05 PM
    • 187 Lines
    Author: pmoreau
  • P76 Splitting 64-bit MAD
    % NV50_PROG_DEBUG=255 nouveau_compiler -a c0 vec_load-64.spv 0 jobs
    Compiling for NVC0
    translating program of type 5
    Parsing SPIR-V generated by 6 (version 10)
    Version 1.0
    ...
    • Jan 23 2016, 7:20 PM
    • 654 Lines
    Author: pmoreau
  • P75 [G96] GPU lockup with MBP switch v5
    [ 0.000000] Initializing cgroup subsys cpuset
    [ 0.000000] Initializing cgroup subsys cpu
    [ 0.000000] Initializing cgroup subsys cpuacct
    [ 0.000000] Linux version 4.4.0-rc6-nouveau-28225-g552da6d (pmoreau@Normandy) (gcc version 5.3.0 (GCC) ) #8 SMP PREEMPT Thu Jan 14 23:17:04 CET 2016
    [ 0.000000] Command line: initrd=\10c24563ac9e431a983ea6b33bb38f27\4.4.0-rc6-nouveau-28225-g552da6d\initrd root=UUID="cd1828b1-4f94-42dc-bebe-c8d9a7767645" rootflags=subvol=@ rw init=/usr/lib/systemd/systemd quiet drm.debug=0xf nouveau.debug=debug,therm=info,i2c=trace,disp=trace log_buf_len=10M systemd.unit=multi-user.target
    ...
    • Jan 19 2016, 10:26 PM
    • 4,909 Lines
    Author: pmoreau
  • P74 Setup OpenCL on Nouveau using SPIR-V
    #!/bin/bash
    # Last updated: 06 May 2017 18:10 GMT+1
    ROOT_DIR=${1}
    ...
    • Jan 18 2016, 10:48 PM
    • 73 Lines
    • Bash Scripting
    Author: pmoreau
  • P73 Set integers size for SPIR-V target in clang
    diff --git a/lib/Basic/Targets.cpp b/lib/Basic/Targets.cpp
    index 4a45c17..ba93541 100644
    --- a/lib/Basic/Targets.cpp
    +++ b/lib/Basic/Targets.cpp
    @@ -6367,7 +6367,7 @@ namespace {
    ...
    • Jan 9 2016, 6:44 PM
    • 13 Lines
    • Diff
    Author: pmoreau
  • P72 Set integers size for SPIR-V target in LLVM
    diff --git a/lib/Target/SPIRV/SPIRVSubtarget.cpp b/lib/Target/SPIRV/SPIRVSubtarget.cpp
    index 95458cd..13fa8fc 100644
    --- a/lib/Target/SPIRV/SPIRVSubtarget.cpp
    +++ b/lib/Target/SPIRV/SPIRVSubtarget.cpp
    @@ -49,7 +49,8 @@ using namespace llvm;
    ...
    • Jan 9 2016, 6:43 PM
    • 14 Lines
    • Diff
    Author: pmoreau
  • P71 clover build fails with clang 3.6
    Making all in src
    make[1]: Entering directory '/home/pmoreau/softwares/mesa-spirv/build/src'
    Making all in .
    make[2]: Entering directory '/home/pmoreau/softwares/mesa-spirv/build/src'
    make[2]: Nothing to be done for 'all-am'.
    ...
    • Dec 30 2015, 10:50 PM
    • 238 Lines
    Author: pmoreau
  • P70 glxinfo -l -s on G96 -- Mesa 11.1.0
    name of display: :0
    display: :0 screen: 0
    direct rendering: Yes
    server glx vendor string: SGI
    server glx version string: 1.4
    ...
    • Dec 28 2015, 4:23 PM
    • 1,498 Lines
    Author: pmoreau
  • P69 RA bails out for hello_world on Tesla
    ./hello_world: /home/pmoreau/userspaces/llvm_spirv/lib/libOpenCL.so.1: no version information available (required by ./hello_world)
    There are 1 platforms.
    There are 1 GPU devices.
    clCreateContext() succeeded.
    clCreateCommandQueue() succeeded.
    ...
    • Dec 15 2015, 10:02 PM
    • 107 Lines
    Author: pmoreau
  • P68 64bit value handling
    Compiling for NVC0
    translating program of type 5
    Parsing SPIR-V generated by 6 (version 8)
    Version 1.0
    ID bound: 10
    ...
    • Dec 15 2015, 2:06 AM
    • 144 Lines
    Author: pmoreau
  • P67 hello_world SPIRV 1.0
    % NV50_PROG_DEBUG=255 ./hello_world
    % 0 jobs
    ./hello_world: /home/pmoreau/userspaces/graphics/lib/libOpenCL.so.1: no version
    information available (required by ./hello_world)
    There are 1 platforms.
    ...
    • Nov 30 2015, 12:36 AM
    • 133 Lines
    Author: pmoreau
  • P66 hello_world.cl
    __kernel void pi(__global float * out)
    {
    out[0] = 3.14159f;
    }
    • Nov 18 2015, 12:30 AM
    • 4 Lines
    Author: pmoreau
  • P65 64-bit MAD/MUL split
    diff --git a/src/gallium/drivers/nouveau/codegen/nv50_ir_build_util.cpp b/src/gallium/drivers/nouveau/codegen/nv50_ir_build_util.cpp
    index 2dd72c3..eab5d05 100644
    --- a/src/gallium/drivers/nouveau/codegen/nv50_ir_build_util.cpp
    +++ b/src/gallium/drivers/nouveau/codegen/nv50_ir_build_util.cpp
    @@ -563,6 +563,7 @@ BuildUtil::split64BitOpPostRA(Function *fn, Instruction *i,
    ...
    • Nov 16 2015, 10:28 PM
    • 57 Lines
    • Diff
    Author: pmoreau
  • P64 `get_local_size()` compilation output
    % NV50_PROG_DEBUG=255 ./get_local_size_3d 0
    % 1 jobs
    ./get_local_size_3d: /opt/cuda/lib64/libOpenCL.so.1: no version information
    available (required by ./get_local_size_3d)
    modprobe: ERROR: could not insert 'nvidia': No such device
    ...
    • Nov 14 2015, 10:17 PM
    • 877 Lines
    Author: pmoreau
  • P63 `get_local_size()` NV50 IR
    nv50_ir::Value*
    Converter::load_opencl_get_local_size(nv50_ir::Value* arg)
    {
    assert(arg != nullptr);
    ...
    • Nov 14 2015, 10:15 PM
    • 89 Lines
    • C++
    Author: pmoreau
  • P62 Tmp
    void func(void)
    {
    int tmp;
    int tmp2;
    ...
    • Nov 14 2015, 6:43 PM
    • 12 Lines
    • C++
    Author: pmoreau
  • P61 get_local_id() NV50 IR codegen
    void
    Converter::load_opencl_get_local_id(unsigned int res_id, nv50_ir::Value* arg)
    {
    assert(arg != nullptr);
    ...
    • Nov 10 2015, 10:24 PM
    • 110 Lines
    • C++
    Author: pmoreau
  • P60 get_local_id NV50_PROG_DEBUG=255
    % NV50_PROG_DEBUG=255 ./get-local-id 5 5
    % 0 jobs
    ./get-local-id: /opt/cuda/lib64/libOpenCL.so.1: no version information
    available (required by ./get-local-id)
    modprobe: ERROR: could not insert 'nvidia': No such device
    ...
    • Nov 10 2015, 10:21 PM
    • 821 Lines
    Author: pmoreau
  • P59 Compiling trivial/compute.c
    CC compute.o
    CCLD quad-tex
    ../../../../../src/gallium/tests/trivial/compute.c:464:49: error: function definition is not allowed here
    void init(void *p, int s, int x, int y) {
    ^
    ...
    • Nov 10 2015, 12:25 AM
    • 90 Lines
    Author: pmoreau
  • P58 get_local_id envydis
    00000000: 10008005 00000003 mov b32 $r1 0x0
    00000008: 10003003 00000780 bra 0x18
    00000010: d03f0009 00000fff and b32 $r2 $r0 0xffff
    00000018: 1000800d 00000003 B mov b32 $r3 0x0
    00000020: 300303fd 640087c8 set $c0 # e u32 $r1 $r3
    ...
    • Nov 8 2015, 11:47 PM
    • 24 Lines
    Author: pmoreau
  • P57 mul signed BT
    * thread #1: tid = 15255, 0x00007ffff78645f8 libc.so.6`__GI_raise + 56, name = 'math-int', stop reason = signal SIGABRT
    * frame #0: 0x00007ffff78645f8 libc.so.6`__GI_raise + 56
    frame #1: 0x00007ffff7865a7a libc.so.6`__GI_abort + 362
    frame #2: 0x00007ffff785d417 libc.so.6`__assert_fail_base + 279
    frame #3: 0x00007ffff785d4c2 libc.so.6`__GI___assert_fail + 66
    ...
    • Nov 8 2015, 12:22 AM
    • 28 Lines
    Author: pmoreau
  • P56 mul NV50 IR
    mul:5 (in %r1 %r2 %r3)
    BB:0 (5 instructions) - df = { }
    0: ld u32 %r1 s[0x10] (0)
    1: ld u32 %r2 s[0x14] (0)
    2: ld u32 %r3 s[0x18] (0)
    ...
    • Nov 7 2015, 11:31 PM
    • 8 Lines
    Author: pmoreau
  • P55 get_local_id_2d OpenCL
    #include <assert.h>
    #include <stdlib.h>
    #include <stdio.h>
    #include <CL/cl.h>
    ...
    • Nov 5 2015, 10:38 PM
    • 63 Lines
    Author: pmoreau
  • P54 get_local_id 2D mmt trace
    LOG: MSG: ==13877== mmaptrace, an MMAP tracer
    LOG: MSG: ==13877== Copyright (C) 2007,2009,2011,2014 and GNU GPL'd, by Dave Airlie, W.J. van der Laan, Marcin Slusarz.
    LOG: MSG: ==13877== Using Valgrind-3.10.0 and LibVEX; rerun with -h for copyright info
    LOG: MSG: ==13877== Command: ./get-local-id-2d
    LOG: MSG: ==13877== Parent PID: 13873
    ...
    • Nov 5 2015, 9:42 PM
    • 29,370 Lines
    Author: pmoreau
  • P53 cupti_query G96
    % LD_LIBRARY_PATH=/opt/cuda/extras/CUPTI/lib64 ./cupti_query 0 jobs
    Assuming default device id 0
    CUDA Device Id : 0
    CUDA Device Name: GeForce 9600M GT
    ...
    • Oct 30 2015, 8:54 PM
    • 19 Lines
    Author: pmoreau
  • P52 cubobjdump of vectorAdd
    Fatbin elf code:
    ================
    arch = sm_11
    code version = [1,2]
    producer = cuda
    ...
    • Oct 28 2015, 11:03 PM
    • 359 Lines
    Author: pmoreau
  • P51 Hello World -- NV50 IR, NV50_PROG_DEBUG=1
    Converting function "pi":
    Converting block 0xc57990
    pi:-1 ()
    BB:0 (4 instructions) - df = { }
    ...
    • Oct 23 2015, 8:41 PM
    • 46 Lines
    Author: pmoreau
  • P50 GALLIUM_HUD="instructions"
    [ 0.000000] Initializing cgroup subsys cpuset
    [ 0.000000] Initializing cgroup subsys cpu
    [ 0.000000] Initializing cgroup subsys cpuacct
    [ 0.000000] Linux version 4.2.3-1-ARCH (builduser@tobias) (gcc version 5.2.0 (GCC) ) #1 SMP PREEMPT Sat Oct 3 18:52:50 CEST 2015
    [ 0.000000] Command line: initrd=\10c24563ac9e431a983ea6b33bb38f27\4.2.3-1-ARCH\initrd root=UUID="cd1828b1-4f94-42dc-bebe-c8d9a7767645" rootflags=subvol=@ rw init=/usr/lib/systemd/systemd quiet
    ...
    • Oct 20 2015, 7:42 PM
    • 3,140 Lines
    Author: pmoreau
  • P49 NV50 MP Counters
    Syntax: GALLIUM_HUD=name1[+name2][...][:value1][,nameI...][;nameJ...]
    Names are identifiers of data sources which will be drawn as graphs
    in panes. Multiple graphs can be drawn in the same pane.
    There can be multiple panes placed in rows and columns.
    ...
    • Oct 20 2015, 5:26 PM
    • 72 Lines
    Author: pmoreau
  • P48 Hello World -- NV50 IR
    pi:-1 ()
    BB:0 (4 instructions) - df = { }
    -> BB:1 (cross)
    0: ld u32 %r0 g[0x70] (0)
    1: mov f32 %r1 3.141590 (0)
    ...
    • Oct 17 2015, 6:50 PM
    • 7 Lines
    Author: pmoreau
  • P47 OpenCL Hello World -- SPIR-V
    % ./nouveau_compiler --spirv -a ac ~/spir-v_examples/hello_world.spirv 0 jobs
    Compiling for NVAC
    File size is 225
    Unknown opcode: 17
    Unknown opcode: 17
    ...
    • Oct 15 2015, 11:31 PM
    • 24 Lines
    Author: pmoreau
  • P46 clxinfo for blob on Titan X
    Number of platforms 1
    Platform Name NVIDIA CUDA
    Platform Vendor NVIDIA Corporation
    Platform Version OpenCL 1.2 CUDA 7.5.0
    Platform Profile FULL_PROFILE
    ...
    • Oct 13 2015, 4:07 PM
    • 110 Lines
    Author: pmoreau
  • P45 CubeMap shader
    #version 330
    uniform samplerCube cubemap;
    in vec3 pass_texcoord;
    ...
    • Oct 12 2015, 7:41 PM
    • 12 Lines
    Author: pmoreau
  • P44 Switch GPUs MBPs -- branch v3
    [ 0.000000] Initializing cgroup subsys cpuset
    [ 0.000000] Initializing cgroup subsys cpu
    [ 0.000000] Initializing cgroup subsys cpuacct
    [ 0.000000] Linux version 4.3.0-rc3-nouveau-12615-ga841baf-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #164 SMP PREEMPT Wed Oct 7 08:36:09 CEST 2015
    [ 0.000000] Command line: initrd=\46c4dc7b7a88458db57d925c24a25f82\4.3.0-rc3-nouveau-12615-ga841baf-dirty\initrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Oct 7 2015, 9:02 AM
    • 4,574 Lines
    Author: pmoreau
  • P43 Vim Syntaxic Coloration for demmio files
    " Vim Syntax File
    " Language: Demmio
    " Maintainer: Pierre Moreau <pierre.morrow@free.fr>
    " Latest Revision: 22 February 2015
    ...
    • Sep 30 2015, 11:36 AM
    • 54 Lines
    Author: pmoreau
  • P42 Vim Syntaxic Coloration for demmt files
    " Vim Syntax File
    " Language: Demmt
    " Maintainer: Pierre Moreau <pierre.morrow@free.fr>
    " Latest Revision: 22 February 2015
    ...
    • Sep 30 2015, 11:36 AM
    • 43 Lines
    Author: pmoreau
  • P41 .ycm_extra_conf.py for Nouveau
    # Generated by YCM Generator at 2015-09-26 16:18:50.372370
    # This file is NOT licensed under the GPLv3, which is the license for the rest
    # of YouCompleteMe.
    #
    ...
    • Sep 29 2015, 11:28 PM
    • 224 Lines
    • Python
    Author: pmoreau
  • P40 .vimrc
    " Vim Configuration File
    " Author: Pierre Moreau <dev@pmoreau.org>
    " Disable Vi compatibility
    ...
    • Sep 29 2015, 11:27 PM
    • 142 Lines
    Author: pmoreau
  • P39 G96 Reclocking v4 -- 0f -- kmsg
    6,0,0,-;Initializing cgroup subsys cpuset
    6,1,0,-;Initializing cgroup subsys cpu
    6,2,0,-;Initializing cgroup subsys cpuacct
    5,3,0,-;Linux version 4.3.0-rc1-nouveau-11624-g5ce033d-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #161 SMP PREEMPT Tue Sep 29 19:07:06 CEST 2015
    6,4,0,-;Command line: initrd=\x5c46c4dc7b7a88458db57d925c24a25f82\x5c4.3.0-rc1-nouveau-11624-g5ce033d-dirty\x5cinitrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 29 2015, 7:46 PM
    • 5,918 Lines
    Author: pmoreau
  • P38 G96 Reclocking v4 -- 0f
    [ 0.000000] Initializing cgroup subsys cpuset
    [ 0.000000] Initializing cgroup subsys cpu
    [ 0.000000] Initializing cgroup subsys cpuacct
    [ 0.000000] Linux version 4.3.0-rc1-nouveau-11624-g5ce033d-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #161 SMP PREEMPT Tue Sep 29 19:07:06 CEST 2015
    [ 0.000000] Command line: initrd=\46c4dc7b7a88458db57d925c24a25f82\4.3.0-rc1-nouveau-11624-g5ce033d-dirty\initrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 29 2015, 7:45 PM
    • 2,972 Lines
    Author: pmoreau
  • P37 lspci -vv 0x154c
    00:00.0 Host bridge: NVIDIA Corporation MCP79 Host Bridge (rev b1)
    Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
    Status: Cap- 66MHz+ UDF- FastB2B+ ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort- >SERR- <PERR- INTx-
    Latency: 0
    ...
    • Sep 27 2015, 2:52 PM
    • 487 Lines
    Author: pmoreau
  • P36 lspci -vv
    00:00.0 Host bridge: NVIDIA Corporation MCP79 Host Bridge (rev b1)
    Control: I/O- Mem+ BusMaster+ SpecCycle- MemWINV- VGASnoop- ParErr- Stepping- SERR- FastB2B- DisINTx-
    Status: Cap- 66MHz+ UDF- FastB2B+ ParErr- DEVSEL=fast >TAbort- <TAbort- <MAbort- >SERR- <PERR- INTx-
    Latency: 0
    ...
    • Sep 27 2015, 1:17 PM
    • 487 Lines
    Author: pmoreau
  • P35 G96 Reclocking v3 -- 03, 05, 0e
    6,0,0,-;Initializing cgroup subsys cpuset
    6,1,0,-;Initializing cgroup subsys cpu
    6,2,0,-;Initializing cgroup subsys cpuacct
    5,3,0,-;Linux version 4.3.0-rc1-nouveau-146569-g935f033-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #159 SMP PREEMPT Sun Sep 27 09:44:26 CEST 2015
    6,4,0,-;Command line: initrd=\x5c46c4dc7b7a88458db57d925c24a25f82\x5c4.3.0-rc1-nouveau-146569-g935f033-dirty\x5cinitrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 27 2015, 10:26 AM
    • 5,710 Lines
    Author: pmoreau
  • P34 G96 Reclocking v3 -- 0f
    6,0,0,-;Initializing cgroup subsys cpuset
    6,1,0,-;Initializing cgroup subsys cpu
    6,2,0,-;Initializing cgroup subsys cpuacct
    5,3,0,-;Linux version 4.3.0-rc1-nouveau-146569-g935f033-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #159 SMP PREEMPT Sun Sep 27 09:44:26 CEST 2015
    6,4,0,-;Command line: initrd=\x5c46c4dc7b7a88458db57d925c24a25f82\x5c4.3.0-rc1-nouveau-146569-g935f033-dirty\x5cinitrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 27 2015, 10:25 AM
    • 4,507 Lines
    Author: pmoreau
  • P33 Mmiotrace Crash
    [ 0.000000] Initializing cgroup subsys cpuset
    [ 0.000000] Initializing cgroup subsys cpu
    [ 0.000000] Initializing cgroup subsys cpuacct
    [ 0.000000] Linux version 4.3.0-rc1-nouveau-146568-ge03fb25-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #156 SMP PREEMPT Fri Sep 25 19:22:52 CEST 2015
    [ 0.000000] Command line: initrd=\46c4dc7b7a88458db57d925c24a25f82\4.3.0-rc1-nouveau-146568-ge03fb25-dirty\initrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 26 2015, 10:35 AM
    • 1,303 Lines
    Author: pmoreau
  • P32 G96 Reclocking
    [ 0.000000] Initializing cgroup subsys cpuset
    [ 0.000000] Initializing cgroup subsys cpu
    [ 0.000000] Initializing cgroup subsys cpuacct
    [ 0.000000] Linux version 4.3.0-rc1-nouveau-146568-ge03fb25-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #156 SMP PREEMPT Fri Sep 25 19:22:52 CEST 2015
    [ 0.000000] Command line: initrd=\46c4dc7b7a88458db57d925c24a25f82\4.3.0-rc1-nouveau-146568-ge03fb25-dirty\initrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 25 2015, 7:52 PM
    • 2,097 Lines
    Author: pmoreau
  • P31 Inform about CSTEP failed parsing
    commit 2f16ac352d8f7a8e183a72fa9ee985a1a7d0cb95
    Author: Pierre Moreau <pierre.morrow@free.fr>
    Date: Thu Sep 24 21:56:16 2015 +0200
    nvbios/power: Inform if parsing CSTEP table failed
    ...
    • Sep 24 2015, 11:12 PM
    • 40 Lines
    Author: pmoreau
  • P30 Fix CSTEP crash
    commit 16ba91316eb45995d435a909a2223d35c84416a9
    Author: Pierre Moreau <dev@pmoreau.org>
    Date: Thu Sep 24 16:20:15 2015 +0200
    nvbios/power: Check if cstep->ent2 is valid before printing
    ...
    • Sep 24 2015, 11:12 PM
    • 22 Lines
    • Diff
    Author: pmoreau
  • P29 nvidia-smi -q
    ==============NVSMI LOG==============
    Timestamp : Thu Sep 24 15:40:24 2015
    Driver Version : 355.11
    ...
    • Sep 24 2015, 3:42 PM
    • 154 Lines
    Author: pmoreau
  • P28 nvidia-smi
    +------------------------------------------------------+
    | NVIDIA-SMI 355.11 Driver Version: 355.11 |
    |-------------------------------+----------------------+----------------------+
    | GPU Name Persistence-M| Bus-Id Disp.A | Volatile Uncorr. ECC |
    | Fan Temp Perf Pwr:Usage/Cap| Memory-Usage | GPU-Util Compute M. |
    ...
    • Sep 24 2015, 3:39 PM
    • 18 Lines
    Author: pmoreau
  • P27 nvidia-settings
    Attribute 'GPUCurrentCoreVoltage' (Sovereign:0.0): 1174570.
    'GPUCurrentCoreVoltage' is an integer attribute.
    'GPUCurrentCoreVoltage' is a read-only attribute.
    'GPUCurrentCoreVoltage' can use the following target types: X Screen, GPU.
    Attribute 'GPUCurrentCoreVoltage' (Sovereign:0[gpu:0]): 1174570.
    ...
    • Sep 24 2015, 3:24 PM
    • 8 Lines
    Author: pmoreau
  • P26 G96 glxinfo -l -s
    name of display: :0
    display: :0 screen: 0
    direct rendering: Yes
    server glx vendor string: SGI
    server glx version string: 1.4
    ...
    • Sep 23 2015, 10:20 PM
    • 1,470 Lines
    Author: pmoreau
  • P25 Xorg.0.log
    [ 11518.367]
    X.Org X Server 1.17.2
    Release Date: 2015-06-16
    [ 11518.367] X Protocol Version 11, Revision 0
    [ 11518.368] Build Operating System: Linux 4.0.4-2-ARCH x86_64
    ...
    • Sep 23 2015, 10:12 PM
    • 426 Lines
    Author: pmoreau
  • P24 strace glxinfo
    % LIBGL_DEBUG=verbose strace -f -e open glxinfo 0 jobs
    open("/etc/ld.so.cache", O_RDONLY|O_CLOEXEC) = 3
    open("/usr/lib/libGL.so.1", O_RDONLY|O_CLOEXEC) = 3
    open("/usr/lib/libX11.so.6", O_RDONLY|O_CLOEXEC) = 3
    open("/usr/lib/libc.so.6", O_RDONLY|O_CLOEXEC) = 3
    ...
    • Sep 23 2015, 10:12 PM
    • 34 Lines
    Author: pmoreau
  • P23 Errors while compiling Clover
    CXX api/libclover_la-device.lo
    In file included from api/context.cpp:23:
    In file included from ./api/util.hpp:30:
    In file included from ./core/property.hpp:28:
    In file included from ./util/range.hpp:29:
    ...
    • Sep 22 2015, 7:01 PM
    • 131 Lines
    Author: pmoreau
  • P22 Reload Nouveau
    #!/bin/bash
    #
    # Reload local Nouveau kernel module.
    #
    ...
    • Sep 22 2015, 6:34 PM
    • 26 Lines
    • Bash Scripting
    Author: pmoreau
  • P21 100% CPU usage in X
    4,34554,173947829,-; [<ffffffff814bfd5f>] vga_switcheroo_reprobe_clients+0x5f/0x80
    4,34555,173947831,-; [<ffffffff8106ac7b>] process_one_work+0x14b/0x440
    4,34556,173947832,-; [<ffffffff8106afb8>] worker_thread+0x48/0x4a0
    4,34557,173947834,-; [<ffffffff8106af70>] ? process_one_work+0x440/0x440
    4,34558,173947835,-; [<ffffffff8106af70>] ? process_one_work+0x440/0x440
    ...
    • Sep 6 2015, 3:39 PM
    • 87,962 Lines
    Author: pmoreau
  • P20 Test 2193551
    6,0,0,-;Initializing cgroup subsys cpuset
    6,1,0,-;Initializing cgroup subsys cpu
    6,2,0,-;Initializing cgroup subsys cpuacct
    5,3,0,-;Linux version 4.2.0-rc8-nouveau-01374-g2193551-dirty (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #145 SMP PREEMPT Sun Sep 6 14:01:28 CEST 2015
    6,4,0,-;Command line: initrd=\x5c46c4dc7b7a88458db57d925c24a25f82\x5c4.2.0-rc8-nouveau-01374-g2193551-dirty\x5cinitrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 6 2015, 2:12 PM
    • 4,265 Lines
    Author: pmoreau
  • P19 Reclocking MCP79
    [ 0.000000] Initializing cgroup subsys cpuset
    [ 0.000000] Initializing cgroup subsys cpu
    [ 0.000000] Initializing cgroup subsys cpuacct
    [ 0.000000] Linux version 4.2.0-rc8-nouveau-66431-g879a37d (pmoreau@testlinux) (gcc version 5.2.0 (GCC) ) #143 SMP PREEMPT Tue Sep 1 11:07:37 CEST 2015
    [ 0.000000] Command line: initrd=\46c4dc7b7a88458db57d925c24a25f82\4.2.0-rc8-nouveau-66431-g879a37d\initrd root=UUID="ba486750-ea35-4585-9da9-dacd96fa4b01" rw init=/usr/lib/systemd/systemd vt.default_utf8=1 log_buf_len=2097152
    ...
    • Sep 2 2015, 2:48 PM
    • 2,095 Lines
    Author: pmoreau
  • P18 Enable EXT_TAG if possible
    diff --git a/drm/nouveau/nouveau_drm.c b/drm/nouveau/nouveau_drm.c
    index ccefb64..31da488 100644
    --- a/drm/nouveau/nouveau_drm.c
    +++ b/drm/nouveau/nouveau_drm.c
    @@ -421,6 +421,15 @@ nouveau_drm_load(struct drm_device *dev, unsigned long flags)
    ...
    • Sep 2 2015, 4:05 AM
    • 36 Lines
    • Diff
    Author: pmoreau
  • P17 nvapeek-lookup.sh
    if [[ -z "${CARD}" ]]; then
    CARD='0'
    fi
    chipset=$(nvalist | head -$((${CARD} + 1)) | tail -1 | cut -d\ -f3)
    ...
    • Sep 2 2015, 2:37 AM
    • 18 Lines
    • Bash Scripting
    Author: pmoreau
  • P16 NV50 IR for P14 (through TGSI)
    MAIN:-1 ()
    BB:0 (10 instructions) - df = { }
    -> BB:1 (tree)
    0: rdsv f32 %r0 sv[POSITION:3] (0)
    1: rcp f32 %r0 %r0 (0)
    ...
    • Aug 12 2015, 9:56 AM
    • 19 Lines
    Author: pmoreau
  • P15 SPIR-V Text for P14
    SPIR-V Module:
    Source = { Source Language: GLSL, Version: 450 }
    Id: 1 Ext Inst Import = { Name: "GLSL.std.450" }
    Memory Model = { Addressing Model: Logical, Memory Model: GLSL450 }
    Entry Point = { Execution Model: Fragment, Entry Point: 4 }
    ...
    • Aug 11 2015, 6:11 PM
    • 19 Lines
    Author: pmoreau
  • P14 Basic GLSL Fragment
    #version 450
    out vec4 color;
    ...
    • Aug 11 2015, 6:10 PM
    • 9 Lines
    Author: pmoreau
Next