debug 241 src/AddImageChecks.cpp debug(3) << "Image " << name << " is only used when " << touched.used << "\n"; debug 245 src/AddImageChecks.cpp debug(3) << "In image " << name << " region touched is:\n"; debug 391 src/AddImageChecks.cpp debug(2) << "Injecting constraints for " << name << "." << i << "\n"; debug 332 src/AssociativeOpsTable.cpp debug(5) << "Returning empty table\n"; debug 338 src/AssociativeOpsTable.cpp debug(5) << "Returning Add root table for type " << exprs[0].type() << "\n"; debug 341 src/AssociativeOpsTable.cpp debug(5) << "Returning Sub root table for type " << exprs[0].type() << "\n"; debug 344 src/AssociativeOpsTable.cpp debug(5) << "Returning Mul root table for type " << exprs[0].type() << "\n"; debug 347 src/AssociativeOpsTable.cpp debug(5) << "Returning Min root table\n"; debug 350 src/AssociativeOpsTable.cpp debug(5) << "Returning Max root table for type " << exprs[0].type() << "\n"; debug 353 src/AssociativeOpsTable.cpp debug(5) << "Returning Select root table for type " << exprs[0].type() << "\n"; debug 356 src/AssociativeOpsTable.cpp debug(5) << "Returning And root table for type " << exprs[0].type() << "\n"; debug 359 src/AssociativeOpsTable.cpp debug(5) << "Returning Or root table for type " << exprs[0].type() << "\n"; debug 362 src/AssociativeOpsTable.cpp debug(5) << "Returning Cast root table for type " << exprs[0].type() << "\n"; debug 368 src/AssociativeOpsTable.cpp debug(7) << "Table size: " << table.size() << "\n"; debug 370 src/AssociativeOpsTable.cpp debug(7) << p; debug 374 src/AssociativeOpsTable.cpp debug(5) << "Returning empty table\n"; debug 65 src/Associativity.cpp debug(5) << "Self-reference of " << op->name debug 73 src/Associativity.cpp debug(5) << " Substituting Call " << op->name << " at value index " debug 104 src/Associativity.cpp debug(5) << "Found associative ops for " << e << " -> " << op debug 112 src/Associativity.cpp debug(5) << "...Skipping match since the x_part is different than expected. " debug 123 src/Associativity.cpp debug(5) << "...Skipping match since the y_part depends on x vars\n"; debug 133 src/Associativity.cpp debug(5) << "...Skipping match since the k_part is not constant\n"; debug 143 src/Associativity.cpp debug(5) << "Adding result: " << iter.first << " -> " << iter.second << "\n"; debug 197 src/Associativity.cpp debug(5) << "Pattern at index " << index << ":\n " << op_x_names[index] debug 360 src/Associativity.cpp debug(5) << "There are cross-dependencies. Need to prove associativity in bulk.\n"; debug 366 src/Associativity.cpp debug(5) << "All tuple elements are independent. Try proving associativity of " debug 375 src/Associativity.cpp debug(5) << "Empty subgraph " << i << "\n"; debug 380 src/Associativity.cpp debug(5) << "Subgraph " << i << " size is " << subgraphs[i].size() << " which is bigger than 2\n"; debug 399 src/Associativity.cpp debug(5) << "Cannot find matching associative ops\n"; debug 403 src/Associativity.cpp debug(5) << "...Proving associativity of subgraph " << i << "\n"; debug 414 src/Associativity.cpp debug(5) << "Conflicting associative ops/identities from different subgraphs\n"; debug 420 src/Associativity.cpp debug(5) << "Conflicting associative x-replacements from different subgraphs\n"; debug 426 src/Associativity.cpp debug(5) << "Conflicting associative y-replacements from different subgraphs\n"; debug 440 src/Associativity.cpp debug(5) << "Found associative ops:\n" << assoc_op << "\n"; debug 513 src/Associativity.cpp debug(5) << "\nExpected op: " << expected_op << "\n"; debug 514 src/Associativity.cpp debug(5) << "Operator: " << result.pattern.ops[i] << "\n"; debug 515 src/Associativity.cpp debug(5) << " identity: " << result.pattern.identities[i] << "\n"; debug 516 src/Associativity.cpp debug(5) << " x: " << result.xs[i].var << " -> " << result.xs[i].expr << "\n"; debug 517 src/Associativity.cpp debug(5) << " y: " << result.ys[i].var << " -> " << result.ys[i].expr << "\n"; debug 1452 src/Bounds.cpp debug(2) << "Bounds on value " << j debug 212 src/BoundsInference.cpp debug(4) << "compute_exprs: all values (size: " << vec.size() << ") " debug 210 src/CSE.cpp debug(4) << "Include: " << e << "; should extract: " << should_extract(e) << "\n"; debug 271 src/CSE.cpp debug(4) << "\n\n\nInput to letify " << e << "\n"; debug 279 src/CSE.cpp debug(4) << "Canonical form without lets " << e << "\n"; debug 294 src/CSE.cpp debug(4) << i << ": " << e.expr << ", " << e.use_count << "\n"; debug 301 src/CSE.cpp debug(4) << "With variables " << e << "\n"; debug 313 src/CSE.cpp debug(4) << "With lets: " << e << "\n"; debug 498 src/CSE.cpp debug(0) << "common_subexpression_elimination test passed\n"; debug 132 src/CanonicalizeGPUVars.cpp debug(5) << "Replacing " << op->name << " with GPU block name " << name << "\n"; debug 135 src/CanonicalizeGPUVars.cpp debug(5) << "Replacing " << op->name << " with GPU thread name " << name << "\n"; debug 44 src/Closure.cpp debug(3) << "Adding buffer " << name << " to closure\n"; debug 56 src/Closure.cpp debug(3) << "Not adding " << name << " to closure\n"; debug 87 src/Closure.cpp debug(3) << "Not adding " << op->name << " to closure\n"; debug 89 src/Closure.cpp debug(3) << "Adding " << op->name << " to closure\n"; debug 799 src/CodeGen_ARM.cpp debug(4) << "Creating call to " << builtin.str() << "\n"; debug 930 src/CodeGen_ARM.cpp debug(4) << "Creating call to " << builtin.str() << "\n"; debug 103 src/CodeGen_GPU_Host.cpp debug(1) << "Constructing OpenGL device codegen\n"; debug 107 src/CodeGen_GPU_Host.cpp debug(1) << "Constructing OpenGL Compute device codegen\n"; debug 111 src/CodeGen_GPU_Host.cpp debug(1) << "Constructing CUDA device codegen\n"; debug 115 src/CodeGen_GPU_Host.cpp debug(1) << "Constructing OpenCL device codegen\n"; debug 119 src/CodeGen_GPU_Host.cpp debug(1) << "Constructing Metal device codegen\n"; debug 184 src/CodeGen_GPU_Host.cpp debug(2) << "Generating init_kernels for " << api_unique_name << "\n"; debug 221 src/CodeGen_GPU_Host.cpp debug(2) << "Kernel launch: " << loop->name << "\n"; debug 229 src/CodeGen_GPU_Host.cpp debug(2) << "Kernel bounds: (" debug 321 src/CodeGen_GPU_Host.cpp debug(2) << "Compiled launch to kernel \"" << kernel_name << "\"\n"; debug 434 src/CodeGen_GPU_Host.cpp debug(4) << "CodeGen_GPU_Host get_user_context returned " << get_user_context() << "\n"; debug 435 src/CodeGen_GPU_Host.cpp debug(3) << "bounds.num_blocks[0] = " << bounds.num_blocks[0] << "\n"; debug 436 src/CodeGen_GPU_Host.cpp debug(3) << "bounds.num_blocks[1] = " << bounds.num_blocks[1] << "\n"; debug 437 src/CodeGen_GPU_Host.cpp debug(3) << "bounds.num_blocks[2] = " << bounds.num_blocks[2] << "\n"; debug 438 src/CodeGen_GPU_Host.cpp debug(3) << "bounds.num_threads[0] = " << bounds.num_threads[0] << "\n"; debug 439 src/CodeGen_GPU_Host.cpp debug(3) << "bounds.num_threads[1] = " << bounds.num_threads[1] << "\n"; debug 440 src/CodeGen_GPU_Host.cpp debug(3) << "bounds.num_threads[2] = " << bounds.num_threads[2] << "\n"; debug 499 src/CodeGen_GPU_Host.cpp debug(4) << "Created device module state global variable\n"; debug 186 src/CodeGen_Hexagon.cpp debug(1) << "Unpredicating loads and stores...\n"; debug 191 src/CodeGen_Hexagon.cpp debug(2) << "Lowering after unpredicating loads/stores:\n" << body << "\n\n"; debug 193 src/CodeGen_Hexagon.cpp debug(1) << "Optimizing shuffles...\n"; debug 197 src/CodeGen_Hexagon.cpp debug(2) << "Lowering after optimizing shuffles:\n" << body << "\n\n"; debug 199 src/CodeGen_Hexagon.cpp debug(1) << "Aligning loads for HVX....\n"; debug 204 src/CodeGen_Hexagon.cpp debug(2) << "Lowering after aligning loads:\n" << body << "\n\n"; debug 206 src/CodeGen_Hexagon.cpp debug(1) << "Carrying values across loop iterations...\n"; debug 210 src/CodeGen_Hexagon.cpp debug(2) << "Lowering after forwarding stores:\n" << body << "\n\n"; debug 213 src/CodeGen_Hexagon.cpp debug(1) << "Eliminating boolean vectors from Hexagon code...\n"; debug 215 src/CodeGen_Hexagon.cpp debug(2) << "Lowering after eliminating boolean vectors: " << body << "\n\n"; debug 218 src/CodeGen_Hexagon.cpp debug(1) << "Optimizing Hexagon instructions...\n"; debug 222 src/CodeGen_Hexagon.cpp debug(1) << "Adding calls to qurt_hvx_lock...\n"; debug 226 src/CodeGen_Hexagon.cpp debug(1) << "Hexagon function body:\n"; debug 227 src/CodeGen_Hexagon.cpp debug(1) << body << "\n"; debug 488 src/CodeGen_LLVM.cpp debug(1) << "Target triple of initial module: " << module->getTargetTriple() << "\n"; debug 525 src/CodeGen_LLVM.cpp debug(1) << "Generating llvm bitcode...\n"; debug 546 src/CodeGen_LLVM.cpp debug(2) << module.get() << "\n"; debug 550 src/CodeGen_LLVM.cpp debug(2) << "Done generating llvm bitcode\n"; debug 610 src/CodeGen_LLVM.cpp debug(1) << "Generating llvm bitcode prolog for function " << name << "...\n"; debug 684 src/CodeGen_LLVM.cpp debug(1) << "Generating llvm bitcode for function " << f.name << "...\n"; debug 892 src/CodeGen_LLVM.cpp debug(4) << "Creating call from wrapper to actual function\n"; debug 980 src/CodeGen_LLVM.cpp debug(3) << "Optimizing module\n"; debug 982 src/CodeGen_LLVM.cpp if (debug::debug_level() >= 3) { debug 997 src/CodeGen_LLVM.cpp debug(2) << "Adding function pass: " << p->getPassName().str() << "\n"; debug 999 src/CodeGen_LLVM.cpp debug(2) << "Adding function pass: " << p->getPassName() << "\n"; debug 1009 src/CodeGen_LLVM.cpp debug(2) << "Adding module pass: " << p->getPassName().str() << "\n"; debug 1011 src/CodeGen_LLVM.cpp debug(2) << "Adding module pass: " << p->getPassName() << "\n"; debug 1044 src/CodeGen_LLVM.cpp debug(3) << "After LLVM optimizations:\n"; debug 1045 src/CodeGen_LLVM.cpp if (debug::debug_level() >= 2) { debug 1072 src/CodeGen_LLVM.cpp if (debug::debug_level() > 0) { debug 1091 src/CodeGen_LLVM.cpp debug(4) << "Codegen: " << e.type() << ", " << e << "\n"; debug 1100 src/CodeGen_LLVM.cpp debug(3) << "Codegen: " << s << "\n"; debug 1890 src/CodeGen_LLVM.cpp debug(4) << "Predicated dense vector store\n\t" << Stmt(op) << "\n"; debug 1936 src/CodeGen_LLVM.cpp debug(4) << "Scalarize predicated vector store\n"; debug 1969 src/CodeGen_LLVM.cpp debug(4) << "Vectorize predicated dense vector load:\n\t" << Expr(load) << "\n"; debug 2039 src/CodeGen_LLVM.cpp debug(4) << "Predicated dense vector load with stride -1\n\t" << Expr(op) << "\n"; debug 2061 src/CodeGen_LLVM.cpp debug(4) << "Scalarize predicated vector load\n\t" << load_expr << "\n"; debug 2531 src/CodeGen_LLVM.cpp debug(1) << "Did not find function " << sub_fn_name debug 2546 src/CodeGen_LLVM.cpp debug(1) << "Did not find function ptr " << extern_sub_fn_name << ", assuming extern \"C\".\n"; debug 2696 src/CodeGen_LLVM.cpp debug(4) << "Adding user_context to " << op->name << " args\n"; debug 2721 src/CodeGen_LLVM.cpp debug(4) << "Did not find " << op->name << ". Declared it extern \"C\".\n"; debug 2723 src/CodeGen_LLVM.cpp debug(4) << "Found " << op->name << "\n"; debug 2750 src/CodeGen_LLVM.cpp debug(4) << "Pointer casting argument to extern call: " debug 2980 src/CodeGen_LLVM.cpp debug(3) << "Entering parallel for loop over " << op->name << "\n"; debug 3054 src/CodeGen_LLVM.cpp debug(4) << "Creating call to do_par_for\n"; debug 3057 src/CodeGen_LLVM.cpp debug(3) << "Leaving parallel for loop over " << op->name << "\n"; debug 363 src/CodeGen_Metal_Dev.cpp debug(2) << "Allocate " << op->name << " on device\n"; debug 365 src/CodeGen_Metal_Dev.cpp debug(3) << "Pushing allocation called " << op->name << " onto the symbol table\n"; debug 413 src/CodeGen_Metal_Dev.cpp debug(2) << "CodeGen_Metal_Dev::compile " << name << "\n"; debug 438 src/CodeGen_Metal_Dev.cpp debug(2) << "Adding Metal kernel " << name << "\n"; debug 568 src/CodeGen_Metal_Dev.cpp debug(2) << "Metal device codegen init_module\n"; debug 620 src/CodeGen_Metal_Dev.cpp debug(1) << "Metal kernel:\n" << str << "\n"; debug 398 src/CodeGen_OpenCL_Dev.cpp debug(2) << "Allocate " << op->name << " on device\n"; debug 400 src/CodeGen_OpenCL_Dev.cpp debug(3) << "Pushing allocation called " << op->name << " onto the symbol table\n"; debug 504 src/CodeGen_OpenCL_Dev.cpp debug(2) << "CodeGen_OpenCL_Dev::compile " << name << "\n"; debug 529 src/CodeGen_OpenCL_Dev.cpp debug(2) << "Adding OpenCL kernel " << name << "\n"; debug 531 src/CodeGen_OpenCL_Dev.cpp debug(2) << "Eliminating bool vectors\n"; debug 533 src/CodeGen_OpenCL_Dev.cpp debug(2) << "After eliminating bool vectors:\n" << s << "\n"; debug 635 src/CodeGen_OpenCL_Dev.cpp debug(2) << "OpenCL device codegen init_module\n"; debug 721 src/CodeGen_OpenCL_Dev.cpp debug(1) << "OpenCL kernel:\n" << str << "\n"; debug 130 src/CodeGen_OpenGLCompute_Dev.cpp debug(4) << "loop extent is " << loop->extent << "\n"; debug 144 src/CodeGen_OpenGLCompute_Dev.cpp debug(4) << "Workgroup size for index " << index << " is " << workgroup_size[index] << "\n"; debug 234 src/CodeGen_OpenGLCompute_Dev.cpp debug(2) << "CodeGen_OpenGLCompute_Dev::compile " << name << "\n"; debug 261 src/CodeGen_OpenGLCompute_Dev.cpp debug(2) << "Adding OpenGLCompute kernel " << name << "\n"; debug 326 src/CodeGen_OpenGLCompute_Dev.cpp debug(2) << "OpenGLCompute: Allocate " << op->name << " of type " << op->type << " on device\n"; debug 352 src/CodeGen_OpenGLCompute_Dev.cpp debug(2) << "OpenGLCompute: Free on device for " << op->name << "\n"; debug 373 src/CodeGen_OpenGLCompute_Dev.cpp debug(1) << "GLSL Compute source:\n" << str << '\n'; debug 91 src/CodeGen_OpenGL_Dev.cpp debug(1) << "Creating GLSL codegen\n"; debug 113 src/CodeGen_OpenGL_Dev.cpp debug(1) << "GLSL source:\n" << str << '\n'; debug 394 src/CodeGen_OpenGL_Dev.cpp debug(1) << "Dropping loop " << loop->name << " (" << loop->min << ", " << loop->extent << ")\n"; debug 690 src/CodeGen_OpenGL_Dev.cpp debug(2) << "Found skipped varying attribute: " << op->args[0] << "\n"; debug 52 src/CodeGen_PTX_Dev.cpp debug(2) << "In CodeGen_PTX_Dev::add_kernel\n"; debug 102 src/CodeGen_PTX_Dev.cpp debug(1) << "Generating llvm bitcode for kernel...\n"; debug 132 src/CodeGen_PTX_Dev.cpp debug(2) << "Done generating llvm bitcode for PTX\n"; debug 192 src/CodeGen_PTX_Dev.cpp debug(2) << "Allocate " << alloc->name << " on device\n"; debug 195 src/CodeGen_PTX_Dev.cpp debug(3) << "Pushing allocation called " << allocation_name << " onto the symbol table\n"; debug 265 src/CodeGen_PTX_Dev.cpp debug(2) << "In CodeGen_PTX_Dev::compile_to_src"; debug 389 src/CodeGen_PTX_Dev.cpp if (debug::debug_level() >= 2) { debug 392 src/CodeGen_PTX_Dev.cpp debug(2) << "Done with CodeGen_PTX_Dev::compile_to_src"; debug 394 src/CodeGen_PTX_Dev.cpp debug(1) << "PTX kernel:\n" << outstr.c_str() << "\n"; debug 133 src/CodeGen_Posix.cpp debug(4) << "cur_stack_alloc_total += " << allocation.stack_bytes << " -> " << cur_stack_alloc_total << " for " << name << "\n"; debug 150 src/CodeGen_Posix.cpp debug(4) << "Reusing freed stack allocation of " << free->stack_bytes debug 161 src/CodeGen_Posix.cpp debug(4) << "Allocating " << stack_bytes << " bytes on the stack for " << name << "\n"; debug 173 src/CodeGen_Posix.cpp debug(4) << "cur_stack_alloc_total += " << allocation.stack_bytes << " -> " << cur_stack_alloc_total << " for " << name << "\n"; debug 187 src/CodeGen_Posix.cpp debug(4) << "Creating call to halide_malloc for allocation " << name debug 190 src/CodeGen_Posix.cpp debug(4) << " x " << e; debug 192 src/CodeGen_Posix.cpp debug(4) << "\n"; debug 229 src/CodeGen_Posix.cpp debug(3) << "Pushing allocation called " << name << " onto the symbol table\n"; debug 243 src/CodeGen_Posix.cpp debug(4) << "cur_stack_alloc_total -= " << alloc.stack_bytes << " -> " << cur_stack_alloc_total << " for " << name << "\n"; debug 6 src/Debug.cpp int debug::debug_level() { debug 47 src/Debug.h class debug { debug 51 src/Debug.h debug(int verbosity) : logging(verbosity <= debug_level()) {} debug 54 src/Debug.h debug &operator<<(T&& x) { debug 41 src/DeepCopy.cpp debug(4) << "Adding deep-copied version to outputs: " << func.name() << "\n"; debug 44 src/DeepCopy.cpp debug(4) << "Adding original version to outputs: " << func.name() << "\n"; debug 17 src/DeviceArgument.cpp debug(2) << "var: " << v.first << "\n"; debug 21 src/DeviceArgument.cpp debug(2) << "buffer: " << b.first << " " << b.second.size; debug 22 src/DeviceArgument.cpp if (b.second.read) debug(2) << " (read)"; debug 23 src/DeviceArgument.cpp if (b.second.write) debug(2) << " (write)"; debug 24 src/DeviceArgument.cpp debug(2) << "\n"; debug 567 src/Elf.cpp debug(2) << "Writing section " << s.get_name() << " at offset " << offset << "\n"; debug 682 src/Elf.cpp debug(2) << "Defining PLT entry for " << sym->get_name() << "\n"; debug 792 src/Elf.cpp debug(2) << "Processing relocations for section " << s.get_name() << "\n"; debug 799 src/Elf.cpp debug(2) << "Using PLT entry " << plt_def->second->get_name() << " for symbol " << sym->get_name() << "\n"; debug 808 src/Elf.cpp debug(2) << "Symbol " << sym->get_name() << " is defined at " << sym_offset << "\n"; debug 815 src/Elf.cpp debug(2) << "Linker returned new relocation type " << new_reloc.get_type() << "\n"; debug 51 src/Error.cpp debug(1) << "User error triggered at " << file << ":" << line << "\n"; debug 53 src/Error.cpp debug(1) << "Condition failed: " << condition_string << "\n"; debug 218 src/Func.cpp Internal::debug(2) << "Adding implicit var " << i << " to call to " << name() << "\n"; debug 248 src/Func.cpp Internal::debug(2) << "Adding implicit var " << i << " to call to " << name() << "\n"; debug 369 src/Func.cpp debug(4) << "...Replace call to Func \"" << c->name << "\" with " debug 443 src/Func.cpp debug(4) << " Splitting " << it->var << " into " << s.outer << " and " << s.inner << "\n"; debug 477 src/Func.cpp debug(4) << " Fusing " << s.outer << " and " << s.inner << " into " << s.old_var << "\n"; debug 510 src/Func.cpp debug(4) << " Purify RVar " << iter->var << " into Var " << s.outer debug 531 src/Func.cpp debug(4) << " Renaming " << iter->var << " into " << s.outer << "\n"; debug 906 src/Func.cpp debug(4) << "In schedule for " << stage_name << ", split " << old << " into " debug 1041 src/Func.cpp debug(4) << "In schedule for " << stage_name << ", fuse " << outer.name() debug 1159 src/Func.cpp debug(4) << "In schedule for " << stage_name << ", purify RVar " debug 1193 src/Func.cpp debug(4) << "In schedule for " << stage_name << ", remove " << var << "\n"; debug 1233 src/Func.cpp debug(4) << " checking fuse " << splits[i-1].inner << " and " debug 1250 src/Func.cpp debug(4) << " splitting " << splits[i-1].old_var << " into " debug 1267 src/Func.cpp debug(4) << " replace/rename " << splits[i-1].old_var debug 1301 src/Func.cpp debug(4) << "In schedule for " << stage_name << ", rename " << old_var.name() debug 2448 src/Func.cpp Internal::debug(2) << "Adding " << count.count << " implicit vars to LHS of " << func.name() << "\n"; debug 303 src/Function.cpp debug(4) << "Deep-copy function contents: \"" << src->name << "\"\n"; debug 904 src/Function.cpp debug(4) << "...Replace call to Func \"" << c->name << "\" with " debug 932 src/Function.cpp debug(4) << "Substituting calls in " << name() << "\n"; debug 594 src/FuseGPUThreadLoops.cpp debug(3) << "Fusing thread block:\n" << body << "\n\n"; debug 599 src/FuseGPUThreadLoops.cpp debug(3) << "Normalized dimensionality:\n" << body << "\n\n"; debug 604 src/FuseGPUThreadLoops.cpp debug(3) << "Injected synchronization:\n" << body << "\n\n"; debug 609 src/FuseGPUThreadLoops.cpp debug(3) << "Replaced for with if:\n" << body << "\n\n"; debug 621 src/FuseGPUThreadLoops.cpp debug(3) << "Rewrapped in for loops:\n" << body << "\n\n"; debug 625 src/FuseGPUThreadLoops.cpp debug(3) << "Add back in shared allocations:\n" << body << "\n\n"; debug 671 src/FuseGPUThreadLoops.cpp debug(3) << "Pulled out shared allocations:\n" << loop << "\n\n"; debug 939 src/Generator.cpp debug(1) << "Generator " << generator_name << " has base_path " << base_path << "\n"; debug 194 src/HexagonOffload.cpp debug(4) << "Relocation in instruction: " << hex(inst) << "\n"; debug 195 src/HexagonOffload.cpp debug(4) << "val: " << hex(val) << "\n"; debug 196 src/HexagonOffload.cpp debug(4) << "mask: " << hex(mask) << "\n"; debug 204 src/HexagonOffload.cpp debug(4) << "Instruction bits: "; debug 206 src/HexagonOffload.cpp debug(4) << (int)((inst >> i) & 1); debug 208 src/HexagonOffload.cpp debug(4) << "\n"; debug 214 src/HexagonOffload.cpp debug(4) << "Duplex!\n"; debug 217 src/HexagonOffload.cpp debug(4) << "Class: " << hex(iclass) << "\n"; debug 218 src/HexagonOffload.cpp debug(4) << "Hi: "; debug 220 src/HexagonOffload.cpp debug(4) << (int)((inst >> i) & 1); debug 222 src/HexagonOffload.cpp debug(4) << "\n"; debug 223 src/HexagonOffload.cpp debug(4) << "Lo: "; debug 225 src/HexagonOffload.cpp debug(4) << (int)((inst >> i) & 1); debug 227 src/HexagonOffload.cpp debug(4) << "\n"; debug 249 src/HexagonOffload.cpp debug(4) << "Instruction-specific case A\n"; debug 253 src/HexagonOffload.cpp debug(4) << "Instruction-specific case B\n"; debug 257 src/HexagonOffload.cpp debug(4) << "Instruction-specific case C\n"; debug 305 src/HexagonOffload.cpp debug(4) << "Relocated instruction: " << hex(inst) << "\n"; debug 326 src/HexagonOffload.cpp debug(2) << "Reusing G=" << G << " for symbol " << sym->get_name() << "\n"; debug 467 src/HexagonOffload.cpp debug(2) << "Adding GOT entry " << G << " for symbol " << sym->get_name() << "\n"; debug 529 src/HexagonOffload.cpp debug(2) << "Adding PLT entry for symbol " << sym.get_name() << "\n"; debug 822 src/HexagonOffload.cpp debug(1) << "Hexagon device code module: " << device_code << "\n"; debug 873 src/HexagonOffload.cpp if (debug::debug_level() >= 2) { debug 874 src/HexagonOffload.cpp debug(0) << "Hexagon device code assembly: " << "\n"; debug 878 src/HexagonOffload.cpp debug(0) << assembly.c_str() << "\n"; debug 913 src/HexagonOffload.cpp debug(1) << "Signing Hexagon code: " << input.pathname() << " -> " << output.pathname() << "\n"; debug 923 src/HexagonOffload.cpp debug(1) << "Signing tool: (" << signer << ")\n"; debug 176 src/HexagonOptimize.cpp debug(3) << "apply_patterns " << x << "\n"; debug 184 src/HexagonOptimize.cpp debug(3) << "matched " << p.pattern << "\n"; debug 185 src/HexagonOptimize.cpp debug(3) << "matches:\n"; debug 187 src/HexagonOptimize.cpp debug(3) << i << "\n"; debug 246 src/HexagonOptimize.cpp debug(3) << "rewrote to: " << x << "\n"; debug 868 src/HexagonOptimize.cpp debug(3) << "rewriting cast to: " << i.first << " from " << cast << "\n"; debug 563 src/IREquality.cpp debug(0) << "ir_equality_test passed\n"; debug 64 src/InjectHostDevBufferCopies.cpp debug(2) << "Buffers to track: Setting Allocate for loop " << op->name << " to " << static_cast<int>(device_api) << "\n"; debug 73 src/InjectHostDevBufferCopies.cpp debug(2) << "Buffers to track: switching from " << static_cast<int>(device_api) << debug 261 src/InjectHostDevBufferCopies.cpp debug(4) << "At loop level " << loop_level << "\n"; debug 270 src/InjectHostDevBufferCopies.cpp debug(4) << "do_copies for " << i.first << "\n" debug 281 src/InjectHostDevBufferCopies.cpp debug(4) << "Device " << static_cast<int>(dev) << " read buffer\n"; debug 294 src/InjectHostDevBufferCopies.cpp debug(4) << "Device " << static_cast<int>(dev) << " wrote buffer\n"; debug 330 src/InjectHostDevBufferCopies.cpp debug(4) << "Needs copy to host\n"; debug 335 src/InjectHostDevBufferCopies.cpp debug(4) << "Invalidating dev_current\n"; debug 353 src/InjectHostDevBufferCopies.cpp debug(4) << "Needs copy to dev\n"; debug 358 src/InjectHostDevBufferCopies.cpp debug(4) << "Invalidating host_current\n"; debug 364 src/InjectHostDevBufferCopies.cpp debug(4) << "Setting host dirty for " << i.first << "\n"; debug 391 src/InjectHostDevBufferCopies.cpp debug(4) << "Injecting device malloc for " << i.first << " on " << debug 400 src/InjectHostDevBufferCopies.cpp debug(4) << "\n"; // Make series of do_copies a bit more readable. debug 416 src/InjectHostDevBufferCopies.cpp debug(4) << "Device " << static_cast<int>(device_api) << " writes buffer " << op->name << "\n"; debug 428 src/InjectHostDevBufferCopies.cpp debug(4) << "Device " << static_cast<int>(device_api) << " reads buffer " << op->name << "\n"; debug 441 src/InjectHostDevBufferCopies.cpp debug(4) << "Adding image read via image_load for " << buffer_var->name << "\n"; debug 452 src/InjectHostDevBufferCopies.cpp debug(4) << "Adding image write via image_store for " << buffer_var->name << "\n"; debug 496 src/InjectHostDevBufferCopies.cpp debug(4) << "Injecting device copy for output " << buf_name << " on " << debug 556 src/InjectHostDevBufferCopies.cpp debug(4) << "Eliding host alloc for " << op->name << "\n"; debug 561 src/InjectHostDevBufferCopies.cpp debug(4) << "Making combined host/device alloc for " << op->name << "\n"; debug 733 src/InjectHostDevBufferCopies.cpp debug(4) << "Switching from device_api " << static_cast<int>(device_api) << " to op->device_api " << debug 762 src/InjectHostDevBufferCopies.cpp debug(4) << "Tracking host <-> dev copies for the following buffers:\n"; debug 764 src/InjectHostDevBufferCopies.cpp debug(4) << i << "\n"; debug 166 src/InjectImageIntrinsics.cpp debug(4) debug 178 src/Introspection.cpp debug(5) << "Loading " << binary << "\n"; debug 230 src/Introspection.cpp debug(2) << "Failed to find HalideIntrospectionCanary::offset_marker\n"; debug 232 src/Introspection.cpp debug(2) << "Failed to find HalideIntrospectionCanary::offset_marker at the expected location\n"; debug 238 src/Introspection.cpp debug(5) << "Program counter adjustment between debug info and actual code: " << pc_adjust << "\n"; debug 281 src/Introspection.cpp debug(5) << "Considering possible global at " << global_pointer << " but global_variables is empty\n"; debug 284 src/Introspection.cpp debug(5) << "Considering possible global at " << global_pointer << "\n"; debug 286 src/Introspection.cpp debug(5) << "Known globals range from " << std::hex << global_variables.front().addr << " to " << global_variables.back().addr << std::dec << "\n"; debug 351 src/Introspection.cpp debug(5) << "Closest global is " << v.name << " at " << std::hex << v.addr << std::dec; debug 353 src/Introspection.cpp debug(5) << " with type " << v.type->name << "\n"; debug 355 src/Introspection.cpp debug(5) << "\n"; debug 372 src/Introspection.cpp debug(5) << "Successful match to array element\n"; debug 386 src/Introspection.cpp debug(5) << "Could not find helper object: " << helper << "\n"; debug 390 src/Introspection.cpp debug(5) << "helper object is " << ptr.name << " at " << std::hex << ptr.addr << std::dec; debug 392 src/Introspection.cpp debug(5) << " with type " << ptr.type->name << "\n"; debug 394 src/Introspection.cpp debug(5) << " with unknown type!\n"; debug 404 src/Introspection.cpp debug(5) << "The object has type: " << object_type->name << "\n"; debug 421 src/Introspection.cpp debug(5) << member.name << " - " << (int)(member.type->type) << "\n"; debug 460 src/Introspection.cpp debug(5) << child.name << " - " << (int)(child.type->type) << "\n"; debug 469 src/Introspection.cpp debug(5) << "Children of heap object of type " << object_type->name << " at " << obj << ":\n"; debug 472 src/Introspection.cpp debug(5) << std::hex << mem.addr << std::dec << ": " << mem.type->name << " " << mem.name << "\n"; debug 484 src/Introspection.cpp debug(5) << "Getting heap member name of " << ptr << "\n"; debug 487 src/Introspection.cpp debug(5) << "No registered heap objects\n"; debug 495 src/Introspection.cpp debug(5) << "No heap objects less than this address\n"; debug 507 src/Introspection.cpp debug(5) << "Not contained in any heap object\n"; debug 520 src/Introspection.cpp debug(5) << "Comparing to member " << obj.members[i].name debug 537 src/Introspection.cpp debug(5) << "Array runs from " << std::hex << array_start_addr << " to " << array_end_addr << "\n"; debug 544 src/Introspection.cpp debug(5) << "Query belongs to this array. Adjusting query address backwards to " debug 554 src/Introspection.cpp debug(5) << "Struct runs from " << std::hex << struct_start_addr << " to " << struct_end_addr << "\n"; debug 561 src/Introspection.cpp debug(5) << "Didn't seem to be any of the members of this heap object\n"; debug 595 src/Introspection.cpp debug(5) << "Walking up the stack\n"; debug 597 src/Introspection.cpp debug(5) << "frame pointer: " << (void *)(fp->frame_pointer) debug 603 src/Introspection.cpp debug(5) << "Bailing out because fp decreased\n"; debug 610 src/Introspection.cpp debug(5) << "Bailing out because we're below the marker\n"; debug 618 src/Introspection.cpp debug(5) << "Bailing out because we didn't even walk up one frame\n"; debug 631 src/Introspection.cpp debug(5) << "Bailing out because we couldn't find the containing function\n"; debug 650 src/Introspection.cpp debug(5) << "Bailing out because containing function used an unknown mechanism for specifying stack offsets\n"; debug 654 src/Introspection.cpp debug(5) << "Searching for var at offset " << offset << "\n"; debug 658 src/Introspection.cpp debug(5) << "Var " << var.name << " is at offset " << var.stack_offset << "\n"; debug 671 src/Introspection.cpp debug(5) << "Skipping var because we're not in any of its live ranges\n"; debug 683 src/Introspection.cpp debug(5) << "Considering match: " << var.type->name << ", " << var.name << "\n"; debug 689 src/Introspection.cpp debug(5) << "Successful match to scalar var\n"; debug 702 src/Introspection.cpp debug(5) << "Successful match to array element\n"; debug 708 src/Introspection.cpp debug(5) << "Failed to find variable at the matching offset with the given type\n"; debug 715 src/Introspection.cpp debug(5) << "Finding source location\n"; debug 718 src/Introspection.cpp debug(5) << "Bailing out because we have no source lines\n"; debug 731 src/Introspection.cpp debug(5) << "Considering address " << ((void *)address) << "\n"; debug 743 src/Introspection.cpp debug(5) << "Skipping function because there's no callq before " << (const void *)(inst_ptr) << "\n"; debug 753 src/Introspection.cpp debug(5) << "Skipping function because we have no debug info for it\n"; debug 757 src/Introspection.cpp debug(5) << "Containing function is " << f->name << "\n"; debug 762 src/Introspection.cpp debug(5) << "Skipping function because it's in the Halide namespace\n"; debug 785 src/Introspection.cpp debug(5) << "Source location is " << oss.str() << "\n"; debug 790 src/Introspection.cpp debug(5) << "Bailing out because we reached the end of the backtrace\n"; debug 880 src/Introspection.cpp debug(1) << "Failed to load binary:" << binary << "\n"; debug 892 src/Introspection.cpp debug(1) << "Failed to load binary:" << binary << "\n"; debug 903 src/Introspection.cpp debug(1) << "Could not load object file: " << binary << "\n"; debug 922 src/Introspection.cpp debug(2) << "Section: " << name.str() << "\n"; debug 941 src/Introspection.cpp debug(2) << "Debugging sections not found\n"; debug 1630 src/Introspection.cpp debug(5) << "Variable with bad abstract origin: " << loc << "\n"; debug 1642 src/Introspection.cpp debug(5) << "var " << var.name << " is at " << var.def_loc << "\n"; debug 1659 src/Introspection.cpp debug(5) << "Global variable with bad spec loc: " << var.spec_loc << "\n"; debug 1771 src/Introspection.cpp debug(5) << "Function " << functions[i].name << ":\n"; debug 1774 src/Introspection.cpp debug(5) << " " << functions[i].variables[j].type->name << " " << functions[i].variables[j].name << "\n"; debug 1788 src/Introspection.cpp debug(5) << "Unpacking members of " << v.name << " at " << std::hex << v.addr << "\n"; debug 1801 src/Introspection.cpp debug(5) << " Member " << mem.name << " goes at " << mem.addr << "\n"; debug 1804 src/Introspection.cpp debug(5) << std::dec; debug 1873 src/Introspection.cpp debug(5) << "Parsing compilation unit from " << off << " to " << unit_end << "\n"; debug 2115 src/Introspection.cpp debug(5) << "Searching for function containing address " << addr << "\n"; debug 2127 src/Introspection.cpp debug(5) << "At function " << functions[mid].name debug 2236 src/Introspection.cpp debug(5) << "Testing compilation unit with offset_marker at " << reinterpret_bits<void *>(calib) << "\n"; debug 2248 src/Introspection.cpp debug(5) << "Failed because frame pointer not saved\n"; debug 2252 src/Introspection.cpp debug(5) << "Failed because offset calibration failed\n"; debug 2258 src/Introspection.cpp debug(5) << "Failed because test routine failed\n"; debug 2262 src/Introspection.cpp debug(5) << "Test passed\n"; debug 77 src/JITModule.cpp debug(1) << "OpenGL support code already linked in...\n"; debug 79 src/JITModule.cpp debug(1) << "Looking for OpenGL support code...\n"; debug 88 src/JITModule.cpp debug(1) << "OpenGL support code already linked in...\n"; debug 90 src/JITModule.cpp debug(1) << "Looking for OpenGL support code...\n"; debug 105 src/JITModule.cpp debug(1) << "Metal framework already linked in...\n"; debug 107 src/JITModule.cpp debug(1) << "Looking for Metal framework...\n"; debug 156 src/JITModule.cpp debug(2) << "JIT Compiling " << name << "\n"; debug 165 src/JITModule.cpp debug(2) << "Function " << name << " is at " << f << "\n"; debug 218 src/JITModule.cpp debug(2) << "Flushing cache from " << (void *)start debug 260 src/JITModule.cpp debug(2) << "Creating new execution engine\n"; debug 261 src/JITModule.cpp debug(2) << "Target triple: " << m->getTargetTriple() << "\n"; debug 319 src/JITModule.cpp debug(1) << "JIT compiling " << module_name << "\n"; debug 336 src/JITModule.cpp debug(2) << "Finalizing object\n"; debug 593 src/JITModule.cpp debug(2) << "Adjusting refcount for module " << module->name << " by " << count << "\n"; debug 25 src/LLVM_Output.cpp Internal::debug(1) << "emit_file.Compiling to native code...\n"; debug 26 src/LLVM_Output.cpp Internal::debug(2) << "Target triple: " << module.getTargetTriple() << "\n"; debug 58 src/LLVM_Runtime_Linker.cpp std::unique_ptr<llvm::Module> get_initmod_##mod(llvm::LLVMContext *context, bool bits_64, bool debug) { \ debug 60 src/LLVM_Runtime_Linker.cpp if (debug) return get_initmod_##mod##_64_debug(context); \ debug 63 src/LLVM_Runtime_Linker.cpp if (debug) return get_initmod_##mod##_32_debug(context); \ debug 619 src/LLVM_Runtime_Linker.cpp bool debug = t.has_feature(Target::Debug); debug 627 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_allocator(c, bits_64, debug)); debug 628 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_error_handler(c, bits_64, debug)); debug 629 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_print(c, bits_64, debug)); debug 631 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_linux_clock(c, bits_64, debug)); debug 633 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_clock(c, bits_64, debug)); debug 635 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_io(c, bits_64, debug)); debug 636 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_tempfile(c, bits_64, debug)); debug 637 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_linux_host_cpu_count(c, bits_64, debug)); debug 638 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_threads(c, bits_64, debug)); debug 639 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_thread_pool(c, bits_64, debug)); debug 640 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_get_symbol(c, bits_64, debug)); debug 642 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_allocator(c, bits_64, debug)); debug 643 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_error_handler(c, bits_64, debug)); debug 644 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_print(c, bits_64, debug)); debug 645 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_osx_clock(c, bits_64, debug)); debug 646 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_io(c, bits_64, debug)); debug 647 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_tempfile(c, bits_64, debug)); debug 648 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_gcd_thread_pool(c, bits_64, debug)); debug 649 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_osx_get_symbol(c, bits_64, debug)); debug 651 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_allocator(c, bits_64, debug)); debug 652 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_error_handler(c, bits_64, debug)); debug 653 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_print(c, bits_64, debug)); debug 655 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_android_clock(c, bits_64, debug)); debug 657 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_clock(c, bits_64, debug)); debug 659 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_android_io(c, bits_64, debug)); debug 660 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_android_tempfile(c, bits_64, debug)); debug 661 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_android_host_cpu_count(c, bits_64, debug)); debug 662 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_threads(c, bits_64, debug)); debug 663 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_thread_pool(c, bits_64, debug)); debug 664 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_get_symbol(c, bits_64, debug)); debug 666 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_allocator(c, bits_64, debug)); debug 667 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_error_handler(c, bits_64, debug)); debug 668 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_print(c, bits_64, debug)); debug 669 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_windows_clock(c, bits_64, debug)); debug 670 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_windows_io(c, bits_64, debug)); debug 671 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_windows_tempfile(c, bits_64, debug)); debug 672 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_windows_threads(c, bits_64, debug)); debug 673 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_thread_pool(c, bits_64, debug)); debug 674 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_windows_get_symbol(c, bits_64, debug)); debug 676 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_mingw_math(c, bits_64, debug)); debug 679 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_allocator(c, bits_64, debug)); debug 680 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_error_handler(c, bits_64, debug)); debug 681 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_print(c, bits_64, debug)); debug 682 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_clock(c, bits_64, debug)); debug 683 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_ios_io(c, bits_64, debug)); debug 684 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_tempfile(c, bits_64, debug)); debug 685 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_gcd_thread_pool(c, bits_64, debug)); debug 687 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_qurt_allocator(c, bits_64, debug)); debug 688 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_error_handler(c, bits_64, debug)); debug 689 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_print(c, bits_64, debug)); debug 690 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_get_symbol(c, bits_64, debug)); debug 691 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_posix_io(c, bits_64, debug)); debug 693 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_fake_thread_pool(c, bits_64, debug)); debug 696 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_noos(c, bits_64, debug)); debug 703 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_buffer_t(c, bits_64, debug)); debug 704 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_destructors(c, bits_64, debug)); debug 720 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_gpu_device_selection(c, bits_64, debug)); debug 721 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_tracing(c, bits_64, debug)); debug 722 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_write_debug_image(c, bits_64, debug)); debug 723 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_cache(c, bits_64, debug)); debug 724 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_to_string(c, bits_64, debug)); debug 726 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_device_interface(c, bits_64, debug)); debug 727 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_metadata(c, bits_64, debug)); debug 728 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_float16_t(c, bits_64, debug)); debug 729 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_old_buffer_t(c, bits_64, debug)); debug 730 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_errors(c, bits_64, debug)); debug 734 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_profiler(c, bits_64, debug)); debug 738 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_msan(c, bits_64, debug)); debug 740 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_msan_stubs(c, bits_64, debug)); debug 767 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_qurt_hvx(c, bits_64, debug)); debug 774 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_prefetch(c, bits_64, debug)); debug 783 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_profiler_inlined(c, bits_64, debug)); debug 789 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_can_use_target(c, bits_64, debug)); debug 791 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_x86_cpu_features(c, bits_64, debug)); debug 795 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_arm_cpu_features(c, bits_64, debug)); debug 797 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_aarch64_cpu_features(c, bits_64, debug)); debug 801 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_mips_cpu_features(c, bits_64, debug)); debug 804 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_powerpc_cpu_features(c, bits_64, debug)); debug 811 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_module_jit_ref_count(c, bits_64, debug)); debug 813 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_module_aot_ref_count(c, bits_64, debug)); debug 819 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_windows_cuda(c, bits_64, debug)); debug 821 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_cuda(c, bits_64, debug)); debug 826 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_windows_opencl(c, bits_64, debug)); debug 828 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_opencl(c, bits_64, debug)); debug 832 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_opengl(c, bits_64, debug)); debug 834 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_linux_opengl_context(c, bits_64, debug)); debug 836 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_osx_opengl_context(c, bits_64, debug)); debug 838 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_android_opengl_context(c, bits_64, debug)); debug 844 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_openglcompute(c, bits_64, debug)); debug 847 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_android_opengl_context(c, bits_64, debug)); debug 849 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_linux_opengl_context(c, bits_64, debug)); debug 851 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_osx_opengl_context(c, bits_64, debug)); debug 858 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_metal(c, bits_64, debug)); debug 860 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_metal_objc_arm(c, bits_64, debug)); debug 862 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_metal_objc_x86(c, bits_64, debug)); debug 868 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_module_jit_ref_count(c, bits_64, debug)); debug 869 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_hexagon_host(c, bits_64, debug)); debug 874 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_matlab(c, bits_64, debug)); debug 879 src/LLVM_Runtime_Linker.cpp modules.push_back(get_initmod_runtime_api(c, bits_64, debug)); debug 247 src/LoopCarry.cpp debug(4) << "About to lift carried values out of stmt: " << orig_stmt << "\n"; debug 258 src/LoopCarry.cpp debug(4) << "Found " << find_loads.result.size() << " loads\n"; debug 303 src/LoopCarry.cpp debug(3) << "Found carried value:\n" debug 344 src/LoopCarry.cpp debug(3) << "Found chain of carried values:\n"; debug 346 src/LoopCarry.cpp debug(3) << i << ": <- " << indices[i] << "\n"; debug 116 src/Lower.cpp debug(1) << "Creating initial loop nests...\n"; debug 118 src/Lower.cpp debug(2) << "Lowering after creating initial loop nests:\n" << s << '\n'; debug 120 src/Lower.cpp debug(1) << "Canonicalizing GPU var names...\n"; debug 122 src/Lower.cpp debug(2) << "Lowering after canonicalizing GPU var names:\n" << s << '\n'; debug 125 src/Lower.cpp debug(1) << "Injecting memoization...\n"; debug 127 src/Lower.cpp debug(2) << "Lowering after injecting memoization:\n" << s << '\n'; debug 129 src/Lower.cpp debug(1) << "Skipping injecting memoization...\n"; debug 132 src/Lower.cpp debug(1) << "Injecting tracing...\n"; debug 134 src/Lower.cpp debug(2) << "Lowering after injecting tracing:\n" << s << '\n'; debug 136 src/Lower.cpp debug(1) << "Adding checks for parameters\n"; debug 138 src/Lower.cpp debug(2) << "Lowering after injecting parameter checks:\n" << s << '\n'; debug 142 src/Lower.cpp debug(1) << "Computing bounds of each function's value\n"; debug 147 src/Lower.cpp debug(1) << "Adding checks for images\n"; debug 149 src/Lower.cpp debug(2) << "Lowering after injecting image checks:\n" << s << '\n'; debug 154 src/Lower.cpp debug(1) << "Performing computation bounds inference...\n"; debug 156 src/Lower.cpp debug(2) << "Lowering after computation bounds inference:\n" << s << '\n'; debug 158 src/Lower.cpp debug(1) << "Performing sliding window optimization...\n"; debug 160 src/Lower.cpp debug(2) << "Lowering after sliding window:\n" << s << '\n'; debug 162 src/Lower.cpp debug(1) << "Performing allocation bounds inference...\n"; debug 164 src/Lower.cpp debug(2) << "Lowering after allocation bounds inference:\n" << s << '\n'; debug 166 src/Lower.cpp debug(1) << "Removing code that depends on undef values...\n"; debug 168 src/Lower.cpp debug(2) << "Lowering after removing code that depends on undef values:\n" << s << "\n\n"; debug 173 src/Lower.cpp debug(1) << "Uniquifying variable names...\n"; debug 175 src/Lower.cpp debug(2) << "Lowering after uniquifying variable names:\n" << s << "\n\n"; debug 177 src/Lower.cpp debug(1) << "Performing storage folding optimization...\n"; debug 179 src/Lower.cpp debug(2) << "Lowering after storage folding:\n" << s << '\n'; debug 181 src/Lower.cpp debug(1) << "Injecting debug_to_file calls...\n"; debug 183 src/Lower.cpp debug(2) << "Lowering after injecting debug_to_file calls:\n" << s << '\n'; debug 185 src/Lower.cpp debug(1) << "Simplifying...\n"; // without removing dead lets, because storage flattening needs the strides debug 187 src/Lower.cpp debug(2) << "Lowering after first simplification:\n" << s << "\n\n"; debug 189 src/Lower.cpp debug(1) << "Injecting prefetches...\n"; debug 191 src/Lower.cpp debug(2) << "Lowering after injecting prefetches:\n" << s << "\n\n"; debug 193 src/Lower.cpp debug(1) << "Dynamically skipping stages...\n"; debug 195 src/Lower.cpp debug(2) << "Lowering after dynamically skipping stages:\n" << s << "\n\n"; debug 197 src/Lower.cpp debug(1) << "Destructuring tuple-valued realizations...\n"; debug 199 src/Lower.cpp debug(2) << "Lowering after destructuring tuple-valued realizations:\n" << s << "\n\n"; debug 202 src/Lower.cpp debug(1) << "Injecting image intrinsics...\n"; debug 204 src/Lower.cpp debug(2) << "Lowering after image intrinsics:\n" << s << "\n\n"; debug 207 src/Lower.cpp debug(1) << "Performing storage flattening...\n"; debug 209 src/Lower.cpp debug(2) << "Lowering after storage flattening:\n" << s << "\n\n"; debug 211 src/Lower.cpp debug(1) << "Unpacking buffer arguments...\n"; debug 213 src/Lower.cpp debug(2) << "Lowering after unpacking buffer arguments...\n"; debug 216 src/Lower.cpp debug(1) << "Rewriting memoized allocations...\n"; debug 218 src/Lower.cpp debug(2) << "Lowering after rewriting memoized allocations:\n" << s << "\n\n"; debug 220 src/Lower.cpp debug(1) << "Skipping rewriting memoized allocations...\n"; debug 227 src/Lower.cpp debug(1) << "Selecting a GPU API for GPU loops...\n"; debug 229 src/Lower.cpp debug(2) << "Lowering after selecting a GPU API:\n" << s << "\n\n"; debug 231 src/Lower.cpp debug(1) << "Injecting host <-> dev buffer copies...\n"; debug 233 src/Lower.cpp debug(2) << "Lowering after injecting host <-> dev buffer copies:\n" << s << "\n\n"; debug 237 src/Lower.cpp debug(1) << "Injecting OpenGL texture intrinsics...\n"; debug 239 src/Lower.cpp debug(2) << "Lowering after OpenGL intrinsics:\n" << s << "\n\n"; debug 244 src/Lower.cpp debug(1) << "Injecting per-block gpu synchronization...\n"; debug 246 src/Lower.cpp debug(2) << "Lowering after injecting per-block gpu synchronization:\n" << s << "\n\n"; debug 249 src/Lower.cpp debug(1) << "Simplifying...\n"; debug 253 src/Lower.cpp debug(2) << "Lowering after second simplifcation:\n" << s << "\n\n"; debug 255 src/Lower.cpp debug(1) << "Reduce prefetch dimension...\n"; debug 257 src/Lower.cpp debug(2) << "Lowering after reduce prefetch dimension:\n" << s << "\n"; debug 259 src/Lower.cpp debug(1) << "Unrolling...\n"; debug 262 src/Lower.cpp debug(2) << "Lowering after unrolling:\n" << s << "\n\n"; debug 264 src/Lower.cpp debug(1) << "Vectorizing...\n"; debug 267 src/Lower.cpp debug(2) << "Lowering after vectorizing:\n" << s << "\n\n"; debug 269 src/Lower.cpp debug(1) << "Detecting vector interleavings...\n"; debug 272 src/Lower.cpp debug(2) << "Lowering after rewriting vector interleavings:\n" << s << "\n\n"; debug 274 src/Lower.cpp debug(1) << "Partitioning loops to simplify boundary conditions...\n"; debug 277 src/Lower.cpp debug(2) << "Lowering after partitioning loops:\n" << s << "\n\n"; debug 279 src/Lower.cpp debug(1) << "Trimming loops to the region over which they do something...\n"; debug 281 src/Lower.cpp debug(2) << "Lowering after loop trimming:\n" << s << "\n\n"; debug 283 src/Lower.cpp debug(1) << "Injecting early frees...\n"; debug 285 src/Lower.cpp debug(2) << "Lowering after injecting early frees:\n" << s << "\n\n"; debug 288 src/Lower.cpp debug(1) << "Injecting profiling...\n"; debug 290 src/Lower.cpp debug(2) << "Lowering after injecting profiling:\n" << s << "\n\n"; debug 294 src/Lower.cpp debug(1) << "Fuzzing floating point stores...\n"; debug 296 src/Lower.cpp debug(2) << "Lowering after fuzzing floating point stores:\n" << s << "\n\n"; debug 299 src/Lower.cpp debug(1) << "Simplifying...\n"; debug 303 src/Lower.cpp debug(1) << "Detecting varying attributes...\n"; debug 305 src/Lower.cpp debug(2) << "Lowering after detecting varying attributes:\n" << s << "\n\n"; debug 307 src/Lower.cpp debug(1) << "Moving varying attribute expressions out of the shader...\n"; debug 309 src/Lower.cpp debug(2) << "Lowering after removing varying attributes:\n" << s << "\n\n"; debug 315 src/Lower.cpp debug(1) << "Lowering after final simplification:\n" << s << "\n\n"; debug 317 src/Lower.cpp debug(1) << "Splitting off Hexagon offload...\n"; debug 319 src/Lower.cpp debug(2) << "Lowering after splitting off Hexagon offload:\n" << s << '\n'; debug 323 src/Lower.cpp debug(1) << "Running custom lowering pass " << i << "...\n"; debug 325 src/Lower.cpp debug(1) << "Lowering after custom pass " << i << ":\n" << s << "\n\n"; debug 356 src/Lower.cpp debug(1) << "Embedding image " << arg.buffer.name() << "\n"; debug 20 src/Module.cpp using Halide::Internal::debug; debug 32 src/Module.cpp debug(1) << "file_unlink: " << f << "\n"; debug 35 src/Module.cpp debug(1) << "dir_rmdir: " << dir_path << "\n"; debug 57 src/Module.cpp debug(1) << "add_temp_object_file: " << name << "\n"; debug 252 src/Module.cpp if (debug::debug_level() >= 2) { debug 253 src/Module.cpp debug(2) << "Submodule assembly for " << name() << ": " << "\n"; debug 257 src/Module.cpp debug(2) << assembly.c_str() << "\n"; debug 322 src/Module.cpp debug(1) << "Module.compile(): object_name " << output_files.object_name << "\n"; debug 335 src/Module.cpp debug(1) << "Module.compile(): temporary object_name " << object_name << "\n"; debug 340 src/Module.cpp debug(1) << "Module.compile(): static_library_name " << output_files.static_library_name << "\n"; debug 345 src/Module.cpp debug(1) << "Module.compile(): assembly_name " << output_files.assembly_name << "\n"; debug 350 src/Module.cpp debug(1) << "Module.compile(): bitcode_name " << output_files.bitcode_name << "\n"; debug 355 src/Module.cpp debug(1) << "Module.compile(): llvm_assembly_name " << output_files.llvm_assembly_name << "\n"; debug 361 src/Module.cpp debug(1) << "Module.compile(): c_header_name " << output_files.c_header_name << "\n"; debug 371 src/Module.cpp debug(1) << "Module.compile(): c_source_name " << output_files.c_source_name << "\n"; debug 380 src/Module.cpp debug(1) << "Module.compile(): stmt_name " << output_files.stmt_name << "\n"; debug 385 src/Module.cpp debug(1) << "Module.compile(): stmt_html_name " << output_files.stmt_html_name << "\n"; debug 428 src/Module.cpp debug(1) << "compile_multitarget: single target is " << base_target.to_string() << "\n"; debug 436 src/Module.cpp const size_t num_threads = (debug::debug_level() > 0) ? 1 : Internal::ThreadPool<void>::num_processors_online(); debug 502 src/Module.cpp debug(1) << "compile_multitarget: compile_sub_target " << o.object_name << "\n"; debug 536 src/Module.cpp debug(1) << "compile_multitarget: compile_standalone_runtime " << o.static_library_name << "\n"; debug 577 src/Module.cpp debug(1) << "compile_multitarget: wrapper " << o.object_name << "\n"; debug 587 src/Module.cpp debug(1) << "compile_multitarget: c_header_name " << o.c_header_name << "\n"; debug 598 src/Module.cpp debug(1) << "compile_multitarget: static_library_name " << output_files.static_library_name << "\n"; debug 148 src/ParallelRVar.cpp debug(3) << "......this thread predicate: " << this_pred << "\n"; debug 149 src/ParallelRVar.cpp debug(3) << "......other thread predicate: " << other_pred << "\n"; debug 153 src/ParallelRVar.cpp debug(3) << "Attempting to falsify: " << hazard << "\n"; debug 158 src/ParallelRVar.cpp debug(3) << "Simplified to: " << hazard << "\n"; debug 468 src/PartitionLoops.cpp debug(3) << "\n\n**** Partitioning loop over " << op->name << "\n"; debug 483 src/PartitionLoops.cpp debug(3) << "\nSimplification: \n" debug 690 src/PartitionLoops.cpp debug(3) << "Partition loop.\n" debug 289 src/Pipeline.cpp debug(1) << "Inferred argument: " << arg.arg.type << " " << arg.arg.name << "\n"; debug 355 src/Pipeline.cpp debug(2) << "Reusing old module\n"; debug 387 src/Pipeline.cpp debug(2) << "jit-compiling for: " << target_arg.to_string() << "\n"; debug 393 src/Pipeline.cpp debug(2) << "Reusing old jit module compiled for :\n" << contents->jit_target.to_string() << "\n"; debug 431 src/Pipeline.cpp debug(4) << "Saving bitcode to: " << file_name << "\n"; debug 622 src/Pipeline.cpp debug(2) << "custom_print: " << (void *)jit_context.handlers.custom_print << '\n' debug 715 src/Pipeline.cpp debug(1) << "JIT input ImageParam argument "; debug 718 src/Pipeline.cpp debug(1) << "JIT input scalar argument "; debug 720 src/Pipeline.cpp debug(1) << "JIT input Image argument "; debug 725 src/Pipeline.cpp debug(1) << arg.arg.name << " @ " << ptr << "\n"; debug 732 src/Pipeline.cpp debug(1) << "JIT output buffer @ " << ptr << ", " << dst[i].data() << "\n"; debug 791 src/Pipeline.cpp debug(2) << "Realizing Pipeline for " << target.to_string() << "\n"; debug 873 src/Pipeline.cpp debug(2) << "Calling jitted function\n"; debug 875 src/Pipeline.cpp debug(2) << "Back from jitted function. Exit status was " << exit_status << "\n"; debug 927 src/Pipeline.cpp debug(1) << "All inputs are bound. No need for bounds inference\n"; debug 942 src/Pipeline.cpp Internal::debug(2) << "Calling jitted function\n"; debug 945 src/Pipeline.cpp Internal::debug(2) << "Back from jitted function\n"; debug 970 src/Pipeline.cpp debug(1) << "Bounds inference converged after " << iter << " iterations\n"; debug 304 src/Prefetch.cpp debug(5) << "\nReduce prefetch to " << max_dim << " dim:\n" debug 367 src/Prefetch.cpp debug(5) << "\nSplit prefetch to max of " << max_byte_size << " bytes:\n" debug 127 src/Profiling.cpp debug(3) << " Allocation on stack: " << op->name << "(" << size << ") in pipeline " << pipeline_name debug 147 src/Profiling.cpp debug(3) << " Allocation on heap: " << op->name << "(" << size << ") in pipeline " << pipeline_name << "\n"; debug 168 src/Profiling.cpp debug(3) << " Free on heap: " << op->name << "(" << alloc.size << ") in pipeline " << pipeline_name << "\n"; debug 178 src/Profiling.cpp debug(3) << " Free on stack: " << op->name << "(" << alloc.size << ") in pipeline " << pipeline_name debug 279 src/ScheduleFunctions.cpp debug(3) << "Value " << i << " = " << v << "\n"; debug 287 src/ScheduleFunctions.cpp debug(3) << "Site " << i << " = " << s << "\n"; debug 696 src/ScheduleFunctions.cpp debug(3) << "InjectRealization of " << func.name() << " entering for loop over " << for_loop->name << "\n"; debug 716 src/ScheduleFunctions.cpp debug(2) << "Injecting realization of " << func.name() << " around node " << Stmt(for_loop) << "\n"; debug 725 src/ScheduleFunctions.cpp debug(3) << "Found compute level\n"; debug 733 src/ScheduleFunctions.cpp debug(3) << "Found store level\n"; debug 1178 src/ScheduleFunctions.cpp debug(1) << "Inlining " << order[i-1] << '\n'; debug 1181 src/ScheduleFunctions.cpp debug(1) << "Injecting realization of " << order[i-1] << '\n'; debug 1187 src/ScheduleFunctions.cpp debug(2) << s << '\n'; debug 196 src/Simplify.cpp debug(1) << spaces << "Simplifying Expr: " << e << "\n"; debug 201 src/Simplify.cpp debug(1) debug 212 src/Simplify.cpp debug(1) << spaces << "Simplifying Stmt: " << s << "\n"; debug 217 src/Simplify.cpp debug(1) debug 4566 src/Simplify.cpp debug(4) << "simplify let " << op->name << " = " << value << " in ... " << op->name << " ...\n"; debug 4663 src/Simplify.cpp debug(4) << "new let " << new_name << " = " << new_value << " in ... " << replacement << " ...\n"; debug 89 src/SimplifySpecializations.cpp debug(1) << "Erasing unreachable specialization (" debug 103 src/SimplifySpecializations.cpp debug(1) << "Replacing default Schedule with const-true specialization for function \"" << name << "\"\n"; debug 350 src/SkipStages.cpp debug(3) << "Finding compute predicate for " << op->name << "\n"; debug 354 src/SkipStages.cpp debug(3) << "Simplifying compute predicate for " << op->name << ": " << find_compute.predicate << "\n"; debug 357 src/SkipStages.cpp debug(3) << "Compute predicate for " << op->name << " : " << compute_predicate << "\n"; debug 369 src/SkipStages.cpp debug(3) << "Finding allocate predicate for " << op->name << "\n"; debug 372 src/SkipStages.cpp debug(3) << "Simplifying allocate predicate for " << op->name << "\n"; debug 375 src/SkipStages.cpp debug(3) << "Allocate predicate for " << op->name << " : " << alloc_predicate << "\n"; debug 380 src/SkipStages.cpp debug(3) << "Done guarding computation for " << op->name << "\n"; debug 463 src/SkipStages.cpp debug(2) << "skip_stages checking " << order[i-1] << "\n"; debug 467 src/SkipStages.cpp debug(2) << "skip_stages can skip " << order[i-1] << "\n"; debug 59 src/SlidingWindow.cpp debug(3) << "Fully expanded " << var->name << " -> " << expr << "\n"; debug 74 src/SlidingWindow.cpp debug(3) << "Expanded " << e << " into " << result << "\n"; debug 123 src/SlidingWindow.cpp debug(3) << "Considering sliding " << func.name() debug 138 src/SlidingWindow.cpp debug(3) << func_args[i] << ":" << min_req << ", " << max_req << "\n"; debug 156 src/SlidingWindow.cpp debug(3) << "Could not perform sliding window optimization of " debug 172 src/SlidingWindow.cpp debug(3) << "Could not performance sliding window optimization of " debug 195 src/SlidingWindow.cpp debug(3) << "Not sliding " << func.name() debug 206 src/SlidingWindow.cpp debug(3) << "Sliding " << func.name() debug 218 src/SlidingWindow.cpp debug(3) << "Not sliding " << func.name() debug 239 src/SlidingWindow.cpp debug(3) << "Sliding " << func.name() << ", " << dim << "\n" debug 292 src/SlidingWindow.cpp debug(3) << "Not entering loop over " << op->name debug 334 src/SlidingWindow.cpp debug(3) << " Doing sliding window analysis over loop: " << op->name << "\n"; debug 383 src/SlidingWindow.cpp debug(3) << "Doing sliding window analysis on realization of " << op->name << "\n"; debug 40 src/Solve.cpp debug(4) << "Mutating " << e << " (" << uses_var << ")\n"; debug 47 src/Solve.cpp debug(4) << "(Miss) Rewrote " << e << " -> " << new_e << " (" << uses_var << ")\n"; debug 52 src/Solve.cpp debug(4) << "(Hit) Rewrote " << e << " -> " << iter->second.expr << " (" << uses_var << ")\n"; debug 105 src/Solve.cpp debug(3) << "Failed to solve: " << e << "\n"; debug 804 src/Solve.cpp debug(3) << "And intersecting: " << Expr(op) << "\n" debug 809 src/Solve.cpp debug(3) << "And union:" << Expr(op) << "\n" debug 822 src/Solve.cpp debug(3) << "Or intersecting:" << Expr(op) << "\n" debug 827 src/Solve.cpp debug(3) << "Or union:" << Expr(op) << "\n" debug 1319 src/Solve.cpp debug(3) << "Solved expr for " << variable << " :\n" debug 1588 src/Solve.cpp debug(0) << "Solve test passed\n"; debug 138 src/StorageFolding.cpp debug(3) << "\nConsidering folding " << func.name() << " over for loop over " << op->name << '\n' debug 205 src/StorageFolding.cpp debug(3) << "Not folding because extent not bounded by a constant not greater than " << max_fold << "\n" debug 212 src/StorageFolding.cpp debug(3) << "Proceeding with factor " << factor << "\n"; debug 234 src/StorageFolding.cpp debug(3) << "Not folding because loop min or max not monotonic in the loop variable\n" debug 310 src/StorageFolding.cpp debug(3) << "Not attempting to fold " << op->name << " because its buffer is used\n"; debug 321 src/StorageFolding.cpp debug(3) << "Attempting to fold " << op->name << "\n"; debug 89 src/TrimNoOps.cpp debug(3) << "Considering store: " << Stmt(op) << "\n"; debug 106 src/TrimNoOps.cpp debug(3) << "Anding condition over domain... " << is_no_op << "\n"; debug 109 src/TrimNoOps.cpp debug(3) << "Condition is now " << condition << "\n"; debug 123 src/TrimNoOps.cpp debug(3) << "About to relax over " << op->name << " : " << condition << "\n"; debug 125 src/TrimNoOps.cpp debug(3) << "Relaxed: " << condition << "\n"; debug 188 src/TrimNoOps.cpp debug(3) << "Attempting to prove: " << test << "\n"; debug 229 src/TrimNoOps.cpp debug(3) << " -> " << test << "\n"; debug 341 src/TrimNoOps.cpp debug(3) << "TrimNoOps found gpu loop var: " << op->name << "\n"; debug 348 src/TrimNoOps.cpp debug(3) << "\n\n ***** Trim no ops in loop over " << op->name << "\n"; debug 352 src/TrimNoOps.cpp debug(3) << "Condition is " << is_no_op.condition << "\n"; debug 355 src/TrimNoOps.cpp debug(3) << "Simplified condition is " << is_no_op.condition << "\n"; debug 372 src/TrimNoOps.cpp debug(3) << "Interval is: " << i.min << ", " << i.max << "\n"; debug 425 src/TrimNoOps.cpp debug(3) << "Rewrote loop.\n" debug 343 src/Util.cpp debug(1) << "temp dir is: " << dir << "\n"; debug 483 src/VaryingAttributes.cpp debug(2) << "Removed varying attribute " << name << "\n"; debug 220 src/VectorizeLoops.cpp debug(3) << "Found gpu loop var: " << op->name << "\n"; debug 679 src/VectorizeLoops.cpp debug(3) << "Vectorizing over " << var << "\n" debug 704 src/VectorizeLoops.cpp debug(4) << "IfThenElse should vectorize predicate over var " << var << "? " << vectorize_predicate << "; cond: " << cond << "\n"; debug 705 src/VectorizeLoops.cpp debug(4) << "Predicated stmt:\n" << predicated_stmt << "\n"; debug 734 src/VectorizeLoops.cpp debug(4) << "...With all_true likely: \n" << stmt << "\n"; debug 740 src/VectorizeLoops.cpp debug(4) << "...Predicated IfThenElse: \n" << stmt << "\n"; debug 745 src/VectorizeLoops.cpp debug(4) << "...Scalarizing vector predicate: \n" << stmt << "\n"; debug 749 src/VectorizeLoops.cpp debug(4) << "...Predicated IfThenElse: \n" << stmt << "\n"; debug 754 src/VectorizeLoops.cpp debug(3) << "Not scalarizing if then else\n"; debug 904 src/VectorizeLoops.cpp debug(0) << e << " -> " << result << "\n"; debug 29 src/WrapCalls.cpp debug(4) << "Merging wrapper of " << in_func.name() << " [" << iter->first.name() debug 35 src/WrapCalls.cpp debug(4) << "Merging wrapper of " << in_func.name() << " [" << wrapped_func.name() debug 82 src/WrapCalls.cpp debug(4) << "Skip over replacing \"" << in_func << "\" with \"" << wrapper.name() << "\"\n"; debug 91 src/WrapCalls.cpp debug(4) << "Global wrapper: replacing reference of \"" debug 97 src/WrapCalls.cpp debug(4) << "Custom wrapper: replacing reference of \"" debug 113 src/WrapCalls.cpp debug(4) << " skip custom wrapper for " << in_func << " [" << wrapped_fname debug 113 src/WrapExternStages.cpp debug(2) << "Wrapped extern call to " << op->name << ":\n" << body << "\n\n"; debug 159 src/WrapExternStages.cpp debug(2) << "Body after wrapping extern calls:\n" << new_body << "\n\n"; debug 244 src/WrapExternStages.cpp debug(2) << "Added legacy wrapper for " << fn.name << ":\n" << body << "\n\n"; debug 19 src/runtime/cache.cpp debug(user_context) << buf_name << ": elem_size " << buf.type.bytes() << " dimensions " << buf.dimensions << ", "; debug 21 src/runtime/cache.cpp debug(user_context) << "(" << buf.dim[i].min debug 25 src/runtime/cache.cpp debug(user_context) << "\n"; debug 37 src/runtime/cache.cpp debug(user_context) << "Key for " << msg << "\n"; debug 59 src/runtime/cache.cpp debug(user_context) << buf << "\n"; debug 423 src/runtime/cache.cpp debug(user_context) << "halide_memoization_cache_store\n"; debug 526 src/runtime/cache.cpp debug(user_context) << "Exiting halide_memoization_cache_store\n"; debug 533 src/runtime/cache.cpp debug(user_context) << "halide_memoization_cache_release\n"; debug 548 src/runtime/cache.cpp debug(user_context) << "Exited halide_memoization_cache_release.\n"; debug 552 src/runtime/cache.cpp debug(NULL) << "halide_memoization_cache_cleanup\n"; debug 42 src/runtime/cuda.cpp debug(user_context) << " Loaded CUDA runtime library: " << lib_names[i] << "\n"; debug 61 src/runtime/cuda.cpp debug(user_context) << " load_libcuda (user_context: " << user_context << ")\n"; debug 198 src/runtime/cuda.cpp debug(user_context) << "CUDA: Multiple CUDA devices detected. Selecting the one with the most cores.\n"; debug 204 src/runtime/cuda.cpp debug(user_context) << " Failed to get device " << i << "\n"; debug 209 src/runtime/cuda.cpp debug(user_context) << " Device " << i << " has " << core_count << " cores\n"; debug 228 src/runtime/cuda.cpp debug(user_context) << " Got device " << dev << "\n"; debug 236 src/runtime/cuda.cpp debug(user_context) << " " << name << "\n"; debug 246 src/runtime/cuda.cpp debug(user_context) << " total memory: " << (int)(memory >> 20) << " MB\n"; debug 295 src/runtime/cuda.cpp debug(user_context) debug 310 src/runtime/cuda.cpp debug(user_context) << " cuCtxCreate " << dev << " -> "; debug 313 src/runtime/cuda.cpp debug(user_context) << get_error_name(err) << "\n"; debug 320 src/runtime/cuda.cpp debug(user_context) << *ctx << "(" << version << ")\n"; debug 367 src/runtime/cuda.cpp debug(user_context) << "CUDA: halide_cuda_initialize_kernels (user_context: " << user_context debug 395 src/runtime/cuda.cpp debug(user_context) << " cuModuleLoadData " << (void *)ptx_src << ", " << size << " -> "; debug 411 src/runtime/cuda.cpp debug(user_context) << get_error_name(err) << "\n"; debug 416 src/runtime/cuda.cpp debug(user_context) << (void *)((*state)->module) << "\n"; debug 422 src/runtime/cuda.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 438 src/runtime/cuda.cpp debug(user_context) debug 452 src/runtime/cuda.cpp debug(user_context) << " cuMemFree " << (void *)(dev_ptr) << "\n"; debug 466 src/runtime/cuda.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 473 src/runtime/cuda.cpp debug(user_context) debug 501 src/runtime/cuda.cpp debug(user_context) << " cuModuleUnload " << state->module << "\n"; debug 514 src/runtime/cuda.cpp debug(user_context) << " cuCtxDestroy " << context << "\n"; debug 528 src/runtime/cuda.cpp debug(user_context) debug 550 src/runtime/cuda.cpp debug(user_context) << " allocating " << *buf << "\n"; debug 557 src/runtime/cuda.cpp debug(user_context) << " cuMemAlloc " << (uint64_t)size << " -> "; debug 560 src/runtime/cuda.cpp debug(user_context) << get_error_name(err) << "\n"; debug 565 src/runtime/cuda.cpp debug(user_context) << (void *)p << "\n"; debug 574 src/runtime/cuda.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 588 src/runtime/cuda.cpp debug(user_context) << " " << copy_name << " " debug 614 src/runtime/cuda.cpp debug(user_context) debug 639 src/runtime/cuda.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 646 src/runtime/cuda.cpp debug(user_context) debug 671 src/runtime/cuda.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 679 src/runtime/cuda.cpp debug(user_context) debug 700 src/runtime/cuda.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 720 src/runtime/cuda.cpp debug(user_context) << "CUDA: halide_cuda_run (" debug 733 src/runtime/cuda.cpp debug(user_context) << "Got context.\n"; debug 741 src/runtime/cuda.cpp debug(user_context) << "Got module " << mod << "\n"; debug 745 src/runtime/cuda.cpp debug(user_context) << "Got function " << f << "\n"; debug 754 src/runtime/cuda.cpp debug(user_context) << " halide_cuda_run " << (int)num_args debug 770 src/runtime/cuda.cpp debug(user_context) << " halide_cuda_run translated arg" << (int)i debug 800 src/runtime/cuda.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 64 src/runtime/device_buffer_utils.h debug(user_context) << "copy_memory: no copy needed as pointers are the same.\n"; debug 114 src/runtime/device_buffer_utils.h debug(NULL) << "c.extent[" << insert << "] = " << (int)(c.extent[insert]) << "\n"; debug 34 src/runtime/device_interface.cpp debug(user_context) << "copy_to_host_already_locked " << buf << " dev_dirty is true\n"; debug 37 src/runtime/device_interface.cpp debug(user_context) << "copy_to_host_already_locked " << buf << " dev_dirty and host_dirty are true\n"; debug 41 src/runtime/device_interface.cpp debug(user_context) << "copy_to_host_already_locked " << buf << " interface is NULL\n"; debug 46 src/runtime/device_interface.cpp debug(user_context) << "copy_to_host_already_locked " << buf << " device copy_to_host returned an error\n"; debug 71 src/runtime/device_interface.cpp debug(NULL) << "halide_copy_to_host " << buf << "\n"; debug 86 src/runtime/device_interface.cpp debug(user_context) debug 93 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf << " interface is NULL\n"; debug 95 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf << " no interface error\n"; debug 102 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf << " flipping buffer to new device\n"; debug 107 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf << " flipping buffer halide_copy_to_host failed\n"; debug 113 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf << " flipping buffer halide_device_free failed\n"; debug 122 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf debug 129 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf << " host is dirty\n"; debug 131 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " << buf << " dev_dirty is true error\n"; debug 138 src/runtime/device_interface.cpp debug(user_context) << "halide_copy_to_device " debug 156 src/runtime/device_interface.cpp debug(user_context) << "halide_device_sync on buffer with no interface\n"; debug 171 src/runtime/device_interface.cpp debug(user_context) << "halide_device_malloc: " << buf debug 200 src/runtime/device_interface.cpp debug(user_context) << "halide_device_free: " << buf debug 241 src/runtime/device_interface.cpp debug(user_context) << "halide_device_and_host_malloc: " << buf debug 271 src/runtime/device_interface.cpp debug(user_context) << "halide_device_and_host_free: " << buf debug 96 src/runtime/hexagon_host.cpp debug(user_context) << " halide_get_library_symbol('" << name << "') -> \n"; debug 98 src/runtime/hexagon_host.cpp debug(user_context) << " " << (void *)sym << "\n"; debug 123 src/runtime/hexagon_host.cpp debug(user_context) << "Hexagon: init_hexagon_runtime (user_context: " << user_context << ")\n"; debug 186 src/runtime/hexagon_host.cpp debug(user_context) << "Hexagon: halide_hexagon_initialize_kernels (user_context: " << user_context debug 207 src/runtime/hexagon_host.cpp debug(user_context) << " allocating module state -> \n"; debug 209 src/runtime/hexagon_host.cpp debug(user_context) << " " << *state << "\n"; debug 218 src/runtime/hexagon_host.cpp debug(user_context) << " halide_remote_initialize_kernels -> "; debug 223 src/runtime/hexagon_host.cpp debug(user_context) << " " << module << "\n"; debug 227 src/runtime/hexagon_host.cpp debug(user_context) << " " << result << "\n"; debug 231 src/runtime/hexagon_host.cpp debug(user_context) << " re-using existing module " << (*state)->module << "\n"; debug 236 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 260 src/runtime/hexagon_host.cpp debug(user_context) << i << ", " << device_handle << "\n"; debug 287 src/runtime/hexagon_host.cpp debug(user_context) << "Hexagon: halide_hexagon_run (" debug 295 src/runtime/hexagon_host.cpp debug(user_context) << " halide_hexagon_remote_get_symbol " << name << " -> "; debug 300 src/runtime/hexagon_host.cpp debug(user_context) << " " << *function << "\n"; debug 345 src/runtime/hexagon_host.cpp debug(user_context) << " halide_hexagon_remote_run -> "; debug 351 src/runtime/hexagon_host.cpp debug(user_context) << " " << result << "\n"; debug 361 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 368 src/runtime/hexagon_host.cpp debug(user_context) debug 377 src/runtime/hexagon_host.cpp debug(user_context) << " halide_remote_release_kernels " << state debug 381 src/runtime/hexagon_host.cpp debug(user_context) << " " << result << "\n"; debug 405 src/runtime/hexagon_host.cpp debug(user_context) debug 426 src/runtime/hexagon_host.cpp debug(user_context) << " allocating buffer of " << (uint64_t)size << " bytes\n"; debug 434 src/runtime/hexagon_host.cpp debug(user_context) << " host_malloc len=" << (uint64_t)size << " -> "; debug 436 src/runtime/hexagon_host.cpp debug(user_context) << " " << ion << "\n"; debug 442 src/runtime/hexagon_host.cpp debug(user_context) << " halide_malloc size=" << (uint64_t)size << " -> "; debug 444 src/runtime/hexagon_host.cpp debug(user_context) << " " << ion << "\n"; debug 465 src/runtime/hexagon_host.cpp debug(user_context) << " host <- " << buf->host << "\n"; debug 470 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 477 src/runtime/hexagon_host.cpp debug(user_context) debug 488 src/runtime/hexagon_host.cpp debug(user_context) << " host_free ion=" << ion << "\n"; debug 491 src/runtime/hexagon_host.cpp debug(user_context) << " halide_free ion=" << ion << "\n"; debug 498 src/runtime/hexagon_host.cpp debug(user_context) << " host <- 0x0\n"; debug 503 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 517 src/runtime/hexagon_host.cpp debug(user_context) debug 534 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 541 src/runtime/hexagon_host.cpp debug(user_context) debug 558 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 565 src/runtime/hexagon_host.cpp debug(user_context) debug 624 src/runtime/hexagon_host.cpp debug(user_context) << "halide_hexagon_device_and_host_malloc called.\n"; debug 633 src/runtime/hexagon_host.cpp debug(user_context) << "halide_hexagon_device_and_host_free called.\n"; debug 643 src/runtime/hexagon_host.cpp debug(user_context) << "halide_hexagon_power_hvx_on\n"; debug 654 src/runtime/hexagon_host.cpp debug(user_context) << " remote_power_hvx_on -> "; debug 656 src/runtime/hexagon_host.cpp debug(user_context) << " " << result << "\n"; debug 664 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 674 src/runtime/hexagon_host.cpp debug(user_context) << "halide_hexagon_power_hvx_off\n"; debug 685 src/runtime/hexagon_host.cpp debug(user_context) << " remote_power_hvx_off -> "; debug 687 src/runtime/hexagon_host.cpp debug(user_context) << " " << result << "\n"; debug 695 src/runtime/hexagon_host.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 709 src/runtime/hexagon_host.cpp debug(user_context) << "halide_hexagon_set_performance_mode\n"; debug 715 src/runtime/hexagon_host.cpp debug(user_context) << " remote_set_performance_mode -> "; debug 717 src/runtime/hexagon_host.cpp debug(user_context) << " " << result << "\n"; debug 730 src/runtime/hexagon_host.cpp debug(user_context) << "halide_hexagon_set_performance\n"; debug 736 src/runtime/hexagon_host.cpp debug(user_context) << " remote_set_performance -> "; debug 746 src/runtime/hexagon_host.cpp debug(user_context) << " " << result << "\n"; debug 224 src/runtime/metal.cpp debug(user_context) << "Metal - Allocating: MTLCreateSystemDefaultDevice\n"; debug 231 src/runtime/metal.cpp debug(user_context) << "Metal - Allocating: new_command_queue\n"; debug 328 src/runtime/metal.cpp debug(user_context) debug 344 src/runtime/metal.cpp debug(user_context) << " allocating " << *buf << "\n"; debug 367 src/runtime/metal.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 374 src/runtime/metal.cpp debug(user_context) << "halide_metal_device_free called on buf " debug 392 src/runtime/metal.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 425 src/runtime/metal.cpp debug(user_context) << "Metal - Allocating: new_library_with_source " << (*state)->library << "\n"; debug 434 src/runtime/metal.cpp debug(user_context) << "Time for halide_metal_initialize_kernels compilation: " << (t_after_compile - t_before_compile) / 1.0e6 << " ms\n"; debug 440 src/runtime/metal.cpp debug(user_context) << "Time for halide_metal_initialize_kernels: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 478 src/runtime/metal.cpp debug(user_context) << "Time for halide_metal_device_sync: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 506 src/runtime/metal.cpp debug(user_context) << "Metal - Releasing: new_library_with_source " << state->library << "\n"; debug 515 src/runtime/metal.cpp debug(user_context) << "Metal - Releasing: new_command_queue " << queue << "\n"; debug 519 src/runtime/metal.cpp debug(user_context) << "Metal - Releasing: MTLCreateSystemDefaultDevice " << device << "\n"; debug 546 src/runtime/metal.cpp debug(user_context) << "halide_metal_copy_to_device dev = " << (void*)buffer->device debug 564 src/runtime/metal.cpp debug(user_context) << "Time for halide_metal_copy_to_device: " debug 596 src/runtime/metal.cpp debug(user_context) << "Time for halide_metal_copy_to_host: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 700 src/runtime/metal.cpp debug(user_context) << "Setting shared memory length to " << shared_mem_bytes << "\n"; debug 704 src/runtime/metal.cpp debug(user_context) << "Dispatching threadgroups (number " << total_dispatches++ << debug 722 src/runtime/metal.cpp debug(user_context) << "Time for halide_metal_device_run: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 729 src/runtime/metal.cpp debug(user_context) << "halide_metal_device_and_host_malloc called.\n"; debug 734 src/runtime/metal.cpp debug(user_context) << "halide_metal_device_and_host_malloc" debug 743 src/runtime/metal.cpp debug(user_context) << "halide_metal_device_and_host_free called.\n"; debug 42 src/runtime/opencl.cpp debug(user_context) << " Loaded OpenCL runtime library: " << lib_names[i] << "\n"; debug 61 src/runtime/opencl.cpp debug(user_context) << " load_libopencl (user_context: " << user_context << ")\n"; debug 233 src/runtime/opencl.cpp debug(user_context) << "CL: validate " << (void *)dev_ptr debug 246 src/runtime/opencl.cpp debug(user_context) debug 295 src/runtime/opencl.cpp debug(user_context) << " clGetPlatformInfo(CL_PLATFORM_NAME) failed: " debug 300 src/runtime/opencl.cpp debug(user_context) << " Got platform '" << platform_name debug 346 src/runtime/opencl.cpp debug(user_context) << " Multiple CL devices detected. Selecting the one with the most cores.\n"; debug 353 src/runtime/opencl.cpp debug(user_context) << " Failed to get info on device " << i << "\n"; debug 356 src/runtime/opencl.cpp debug(user_context) << " Device " << i << " has " << core_count << " cores\n"; debug 362 src/runtime/opencl.cpp debug(user_context) << " Selected device " << device << "\n"; debug 413 src/runtime/opencl.cpp debug(user_context) debug 432 src/runtime/opencl.cpp debug(user_context) << " clCreateContext -> "; debug 435 src/runtime/opencl.cpp debug(user_context) << get_opencl_error_name(err); debug 440 src/runtime/opencl.cpp debug(user_context) << *ctx << "\n"; debug 443 src/runtime/opencl.cpp debug(user_context) << " clCreateCommandQueue "; debug 446 src/runtime/opencl.cpp debug(user_context) << get_opencl_error_name(err); debug 451 src/runtime/opencl.cpp debug(user_context) << *q << "\n"; debug 471 src/runtime/opencl.cpp debug(user_context) debug 485 src/runtime/opencl.cpp debug(user_context) << " clReleaseMemObject " << (void *)dev_ptr << "\n"; debug 500 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 508 src/runtime/opencl.cpp debug(user_context) debug 574 src/runtime/opencl.cpp debug(user_context) << " clCreateProgramWithSource -> "; debug 577 src/runtime/opencl.cpp debug(user_context) << get_opencl_error_name(err) << "\n"; debug 582 src/runtime/opencl.cpp debug(user_context) << (void *)program << "\n"; debug 586 src/runtime/opencl.cpp debug(user_context) << " clBuildProgram " << (void *)program debug 613 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 621 src/runtime/opencl.cpp debug(user_context) << "CL: halide_opencl_device_sync (user_context: " << user_context << ")\n"; debug 639 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 646 src/runtime/opencl.cpp debug(user_context) debug 671 src/runtime/opencl.cpp debug(user_context) << " clReleaseProgram " << state->program << "\n"; debug 681 src/runtime/opencl.cpp debug(user_context) << " clReleaseCommandQueue " << command_queue << "\n"; debug 686 src/runtime/opencl.cpp debug(user_context) << " clReleaseContext " << context << "\n"; debug 699 src/runtime/opencl.cpp debug(user_context) debug 720 src/runtime/opencl.cpp debug(user_context) << " allocating " << *buf << "\n"; debug 727 src/runtime/opencl.cpp debug(user_context) << " clCreateBuffer -> " << (int)size << " "; debug 730 src/runtime/opencl.cpp debug(user_context) << get_opencl_error_name(err) << "\n"; debug 735 src/runtime/opencl.cpp debug(user_context) << (void *)dev_ptr << "\n"; debug 742 src/runtime/opencl.cpp debug(user_context) debug 748 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 764 src/runtime/opencl.cpp debug(user_context) << " " << copy_name << " " debug 791 src/runtime/opencl.cpp debug(user_context) << " " << copy_name << " " debug 838 src/runtime/opencl.cpp debug(user_context) debug 868 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 875 src/runtime/opencl.cpp debug(user_context) debug 905 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 924 src/runtime/opencl.cpp debug(user_context) debug 947 src/runtime/opencl.cpp debug(user_context) << " clCreateKernel " << entry_name << " -> "; debug 950 src/runtime/opencl.cpp debug(user_context) << get_opencl_error_name(err) << "\n"; debug 957 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_create_kernel - t_before) / 1.0e6 << " ms\n"; debug 968 src/runtime/opencl.cpp debug(user_context) << " clSetKernelArg " << i debug 978 src/runtime/opencl.cpp debug(user_context) << "Mapped dev handle is: " << (void *)opencl_handle << "\n"; debug 997 src/runtime/opencl.cpp debug(user_context) debug 1007 src/runtime/opencl.cpp debug(user_context) debug 1016 src/runtime/opencl.cpp debug(user_context) << get_opencl_error_name(err) << "\n"; debug 1023 src/runtime/opencl.cpp debug(user_context) << " Releasing kernel " << (void *)f << "\n"; debug 1025 src/runtime/opencl.cpp debug(user_context) << " clReleaseKernel finished" << (void *)f << "\n"; debug 1034 src/runtime/opencl.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 << " ms\n"; debug 284 src/runtime/opengl.cpp debug(NULL) << "Saved OpenGL state\n"; debug 291 src/runtime/opengl.cpp debug(NULL) << "Restoring OpenGL state\n"; debug 355 src/runtime/opengl.cpp debug(user_context) << *buf << "\n"; debug 362 src/runtime/opengl.cpp debug(user_context) << ((type == GL_VERTEX_SHADER) ? "GL_VERTEX_SHADER" : "GL_FRAGMENT_SHADER") debug 375 src/runtime/opengl.cpp debug(user_context) << "Halide GLSL: passed shader source is empty, using default.\n"; debug 459 src/runtime/opengl.cpp debug(user_context) << "Compiling GLSL kernel (size = " << size << "):\n"; debug 710 src/runtime/opengl.cpp debug(user_context) debug 755 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_release\n"; debug 775 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_device_release: Deleting texture " << tex->id << "\n"; debug 787 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_release: deleted " debug 1035 src/runtime/opengl.cpp debug(user_context) << "Allocated texture " << tex debug 1078 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_device_free: Deleting texture " << tex << "\n"; debug 1180 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_copy_to_device: called for HALIDE_OPENGL_RENDER_TARGET\n"; debug 1184 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_copy_to_device: " << tex << "\n"; debug 1214 src/runtime/opengl.cpp debug(user_context) debug 1278 src/runtime/opengl.cpp debug(user_context) << "halide_copy_to_host: texture " << tex << "\n"; debug 1288 src/runtime/opengl.cpp debug(user_context) << "halide_copy_to_host: HALIDE_OPENGL_RENDER_TARGET\n"; debug 1315 src/runtime/opengl.cpp debug(user_context) << "ReadPixels does not support our format; falling back to GL_RGBA\n"; debug 1339 src/runtime/opengl.cpp debug(user_context) << "ReadPixels(1) time: "<<(t2-t1)/1e3<<"usec\n"; debug 1342 src/runtime/opengl.cpp debug(user_context) debug 1359 src/runtime/opengl.cpp debug(user_context)<<"ReadPixels(2) time: "<<(t2-t1)/1e3<<"usec\n"; debug 1384 src/runtime/opengl.cpp debug(user_context)<<"deinterleave time: "<<(t4-t3)/1e3<<"usec\n"; debug 1679 src/runtime/opengl.cpp debug(user_context) debug 1755 src/runtime/opengl.cpp debug(user_context) << "output_extent: " << output_extent[0] << "," << output_extent[1] << "\n"; debug 1756 src/runtime/opengl.cpp debug(user_context) << "output_min: " << output_min[0] << "," << output_min[1] << "\n"; debug 1790 src/runtime/opengl.cpp debug(user_context) << "Vertex buffer:"; debug 1793 src/runtime/opengl.cpp debug(user_context) << "\n"; debug 1795 src/runtime/opengl.cpp debug(user_context) << vertex_buffer[i] << " "; debug 1797 src/runtime/opengl.cpp debug(user_context) << "\n"; debug 1798 src/runtime/opengl.cpp debug(user_context) << "\n"; debug 1800 src/runtime/opengl.cpp debug(user_context) << "Element buffer:"; debug 1803 src/runtime/opengl.cpp debug(user_context) << "\n"; debug 1805 src/runtime/opengl.cpp debug(user_context) << element_buffer[i] << " "; debug 1807 src/runtime/opengl.cpp debug(user_context) << "\n"; debug 1901 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_device_sync: took " << (t1 - t0) / 1e3 << "usec\n"; debug 1911 src/runtime/opengl.cpp debug(user_context) << "In initialize_kernels\n"; debug 2034 src/runtime/opengl.cpp debug(user_context) << "Could not link GLSL program:\n" << log << "\n"; debug 2061 src/runtime/opengl.cpp debug(user_context) << "halide_opengl_context_lost\n"; debug 129 src/runtime/openglcompute.cpp debug(user_context) debug 183 src/runtime/openglcompute.cpp debug(user_context) << "Halide running on "<< global_state.GetString(GL_VERSION) << "\n"; debug 198 src/runtime/openglcompute.cpp debug(user_context) << "OpenGLCompute: halide_openglcompute_device_release(user_context: " debug 223 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 237 src/runtime/openglcompute.cpp debug(user_context) << "OpenGLCompute: halide_openglcompute_device_malloc (user_context: " debug 249 src/runtime/openglcompute.cpp debug(user_context) << "openglcompute_device_malloc: This buffer already has a " debug 259 src/runtime/openglcompute.cpp debug(user_context) << " allocating buffer, " debug 271 src/runtime/openglcompute.cpp debug(user_context) << "openglcompute_device_malloc: initialization completed.\n"; debug 292 src/runtime/openglcompute.cpp debug(user_context) << "Allocated dev_buffer(i.e. vbo) " << the_buffer << "\n"; debug 296 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 318 src/runtime/openglcompute.cpp debug(user_context) << "OGLC: halide_openglcompute_device_free (" debug 331 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 350 src/runtime/openglcompute.cpp debug(user_context) << "OGLC: halide_openglcompute_copy_to_device (" debug 363 src/runtime/openglcompute.cpp debug(user_context) << " copied " << ((unsigned)size) << " bytes from " << buf->host << " to the device.\n"; debug 367 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 388 src/runtime/openglcompute.cpp debug(user_context) << "OGLC: halide_openglcompute_copy_to_host (" debug 405 src/runtime/openglcompute.cpp debug(user_context) << " copied " << (unsigned)size << " bytes to the host.\n"; debug 409 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 435 src/runtime/openglcompute.cpp debug(user_context) debug 471 src/runtime/openglcompute.cpp debug(user_context) << " args " << i debug 504 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 523 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 595 src/runtime/openglcompute.cpp debug(user_context) << "Compute shader source for " << kernel_name << " :" << src; debug 596 src/runtime/openglcompute.cpp debug(user_context) << "\n"; debug 638 src/runtime/openglcompute.cpp debug(user_context) << "Could not link GLSL program:\n" << log << "\n"; debug 649 src/runtime/openglcompute.cpp debug(user_context) << " Time: " << (t_after - t_before) / 1.0e6 debug 23 src/runtime/posix_get_symbol.cpp debug(NULL) << "dlerror: " << dlerror() << "\n"; debug 28 src/runtime/qurt_hvx.cpp debug(user_context) << "QuRT: qurt_hvx_lock(" << mode << ") ->\n"; debug 30 src/runtime/qurt_hvx.cpp debug(user_context) << " " << result << "\n"; debug 40 src/runtime/qurt_hvx.cpp debug(user_context) << "QuRT: qurt_hvx_unlock ->\n"; debug 42 src/runtime/qurt_hvx.cpp debug(user_context) << " " << result << "\n";