Generic test bench for loads/stores. Change-Id: I1193581f8240826da99592c6193e58ece7edfb04

diff --git a/hdl/chisel/src/bus/BUILD b/hdl/chisel/src/bus/BUILD
index 9a6f1e3..0a257c2 100644
--- a/hdl/chisel/src/bus/BUILD
+++ b/hdl/chisel/src/bus/BUILD

@@ -100,6 +100,7 @@
 AXI2TLUL_TESTCASES = [
     "test_write_request",
     "test_read_request",
+    "test_read_error",
 ]
 # END_TESTCASES_FOR_axi2tlul_cocotb_test
 

diff --git a/tests/cocotb/BUILD b/tests/cocotb/BUILD
index 206b156..5259869 100644
--- a/tests/cocotb/BUILD
+++ b/tests/cocotb/BUILD

@@ -182,6 +182,7 @@
     "load16_segment2_stride6_m1",
     "load8_indexed_m1",
     "store8_indexed_m1",
+    "load_store8_test",
 ]
 # END_TESTCASES_FOR_rvv_load_store_test
 
@@ -189,6 +190,7 @@
 RVV_ARITHMETIC_TESTCASES = [
     "arithmetic_m1_vanilla_ops",
     "reduction_m1_vanilla_ops",
+    "widen_math_ops_test_impl",
 ]
 # END_TESTCASES_FOR_rvv_arithmetic_cocotb_test
 

diff --git a/tests/cocotb/rvv/load_store/BUILD b/tests/cocotb/rvv/load_store/BUILD
index aa9dd02..167cd30 100644
--- a/tests/cocotb/rvv/load_store/BUILD
+++ b/tests/cocotb/rvv/load_store/BUILD

@@ -56,6 +56,9 @@
         "load8_stride2_mf4": {
             "srcs": ["load8_stride2_mf4.cc"],
         },
+        "load_store8_test": {
+            "srcs": ["load_store8_test.cc"],
+        },
         "load_store8_unit_m2": {
             "srcs": ["load_store8_unit_m2.cc"],
         },
@@ -101,6 +104,7 @@
         ":load8_stride2_m1.elf",
         ":load8_stride2_m1_partial.elf",
         ":load8_stride2_mf4.elf",
+        ":load_store8_test.elf",
         ":load_store8_unit_m2.elf",
         ":load_store16_unit_m2.elf",
         ":load_store32_unit_m2.elf",

diff --git a/tests/cocotb/rvv/load_store/load_store8_test.cc b/tests/cocotb/rvv/load_store/load_store8_test.cc
new file mode 100644
index 0000000..7b0f3cd
--- /dev/null
+++ b/tests/cocotb/rvv/load_store/load_store8_test.cc

@@ -0,0 +1,32 @@
+// Copyright 2025 Google LLC
+//
+// Licensed under the Apache License, Version 2.0 (the "License");
+// you may not use this file except in compliance with the License.
+// You may obtain a copy of the License at
+//
+//     http://www.apache.org/licenses/LICENSE-2.0
+//
+// Unless required by applicable law or agreed to in writing, software
+// distributed under the License is distributed on an "AS IS" BASIS,
+// WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
+// See the License for the specific language governing permissions and
+// limitations under the License.
+
+#include <riscv_vector.h>
+#include <stdint.h>
+
+// A fully parameterized test that executes a m1 unit load/store pair. Addresses
+// can be overridden with the `in_ptr` and `out_ptr` variables and data size
+// can be overridden via the `vl` parameter.
+
+uint8_t buffer[4096] __attribute__((section(".data")));
+uint8_t* in_ptr __attribute__((section(".data"))) = &(buffer[0]);
+uint8_t* out_ptr __attribute__((section(".data"))) = &(buffer[0]);
+size_t vl __attribute__((section(".data"))) = 16 ;
+
+int main() {
+  vuint8m1_t v = __riscv_vle8_v_u8m1(in_ptr, vl);
+  __riscv_vse8_v_u8m1(out_ptr, v, vl);
+
+  return 0;
+}

diff --git a/tests/cocotb/rvv_load_store_test.py b/tests/cocotb/rvv_load_store_test.py
index 5fcdd5d..78da0b4 100644
--- a/tests/cocotb/rvv_load_store_test.py
+++ b/tests/cocotb/rvv_load_store_test.py

@@ -382,3 +382,29 @@
         elf_name = 'store8_indexed_m1.elf',
         dtype = np.uint8,
     )
+
+@cocotb.test()
+async def load_store8_test(dut):
+    """Testbench to test RVV load."""
+    fixture = await Fixture.Create(dut)
+    r = runfiles.Create()
+    await fixture.load_elf_and_lookup_symbols(
+        r.Rlocation('kelvin_hw/tests/cocotb/rvv/load_store/load_store8_test.elf'),
+        ['buffer', 'in_ptr', 'out_ptr', 'vl'],
+    )
+
+    vl = 16
+    input_data = np.random.randint(0, 255, vl, dtype=np.uint8)
+    target_in_addr = fixture.symbols['buffer'] + 16
+    target_out_addr = fixture.symbols['buffer'] + 64
+
+    await fixture.core_mini_axi.write(target_in_addr, input_data)
+    await fixture.write('in_ptr', np.array([target_in_addr], dtype=np.uint32))
+    await fixture.write('out_ptr', np.array([target_out_addr], dtype=np.uint32))
+    await fixture.write('vl', np.array([vl], dtype=np.uint32))
+
+    await fixture.run_to_halt()
+
+    routputs = (await fixture.core_mini_axi.read(target_out_addr, vl)).view(
+        np.uint8)
+    assert (input_data == routputs).all()