diff --git a/stimBuffApis/livoxGen1/collateDgrams.cl b/stimBuffApis/livoxGen1/collateDgrams.cl
index 36a83f6..285db78 100644
--- a/stimBuffApis/livoxGen1/collateDgrams.cl
+++ b/stimBuffApis/livoxGen1/collateDgrams.cl
@@ -1,3 +1,3 @@
 __kernel void collate(__global uchar* assembly, __global uchar* collation) {
-	// Placeholder kernel - will be replaced with actual collation logic
+	// Placeholder kernel - will be replaced with actual collation logic.
 }
diff --git a/stimBuffApis/livoxGen1/openClKernels.cl.S b/stimBuffApis/livoxGen1/openClKernels.cl.S
index d6d17a6..4d4c8e6 100644
--- a/stimBuffApis/livoxGen1/openClKernels.cl.S
+++ b/stimBuffApis/livoxGen1/openClKernels.cl.S
@@ -1,17 +1,17 @@
 	.section .rodata
 	.global collateKernelStart
-	.global collateKernelEnd
 	.global collateKernelNBytes
 	.type collateKernelStart, @object
-	.type collateKernelEnd, @object
 	.type collateKernelNBytes, @object
 
 collateKernelStart:
 	.incbin "collateDgrams.cl"
+	.size collateKernelStart, . - collateKernelStart
 collateKernelEnd:
 
 	.section .data
 collateKernelNBytes:
 	.long collateKernelEnd - collateKernelStart
+	.size collateKernelNBytes, 4
 
 	.section .note.GNU-stack,"",@progbits
diff --git a/stimBuffApis/livoxGen1/openClKernels.h b/stimBuffApis/livoxGen1/openClKernels.h
index 86fa595..84e549c 100644
--- a/stimBuffApis/livoxGen1/openClKernels.h
+++ b/stimBuffApis/livoxGen1/openClKernels.h
@@ -3,15 +3,16 @@
 
 #include <cstdint>
 
-namespace smo {
-namespace stim_buff {
+#ifdef __cplusplus
+extern "C" {
+#endif
 
-// External symbols for collate kernel
+// External symbols for collate kernel (unmangled, not namespaced)
 extern const char collateKernelStart[];
-extern const char collateKernelEnd[];
 extern const uint32_t collateKernelNBytes;
 
-} // namespace stim_buff
-} // namespace smo
+#ifdef __cplusplus
+} // extern "C"
+#endif
 
 #endif // _LIVOX_GEN1_OPENCL_KERNELS_H