xemu/accel/stubs
William Roche 06152b89db migration: prevent migration when VM has poisoned memory
A memory page poisoned from the hypervisor level is no longer readable.
The migration of a VM will crash Qemu when it tries to read the
memory address space and stumbles on the poisoned page with a similar
stack trace:

Program terminated with signal SIGBUS, Bus error.
  _mm256_loadu_si256
  buffer_zero_avx2
  select_accel_fn
  buffer_is_zero
  save_zero_page
  ram_save_target_page_legacy
  ram_save_host_page
  ram_find_and_save_block
  ram_save_iterate
  qemu_savevm_state_iterate
 migration_iteration_run
 migration_thread
 qemu_thread_start

To avoid this VM crash during the migration, prevent the migration
when a known hardware poison exists on the VM.

Signed-off-by: William Roche <william.roche@oracle.com>
Link: https://lore.kernel.org/r/20240130190640.139364-2-william.roche@oracle.com
Signed-off-by: Peter Xu <peterx@redhat.com>
2024-02-05 14:41:58 +08:00
..
kvm-stub.c migration: prevent migration when VM has poisoned memory 2024-02-05 14:41:58 +08:00
meson.build accel: Rename accel_softmmu* -> accel_system* 2023-10-07 19:02:57 +02:00
tcg-stub.c accel/tcg: Factor tcg_cpu_reset_hold() out 2023-11-07 12:13:27 +01:00
xen-stub.c qapi: Restrict Xen migration commands to migration.json 2020-10-21 05:00:44 +02:00